From e0187ba405b116870f9bbbbfa9d5055ef557c782 Mon Sep 17 00:00:00 2001
From: Vladislav Sytchenko <vladislav.sytchenko@amd.com>
Date: Mon, 23 Mar 2020 16:26:21 -0400
Subject: [PATCH] Add initial entry points for mipmapped array API

Change-Id: Icd59cc7323ddcb6773da6105260415a1e6f4cdcb
---
 include/hip/hcc_detail/hip_runtime_api.h | 13 +++++++
 vdi/hip_hcc.def.in                       |  6 ++++
 vdi/hip_hcc.map.in                       |  6 ++++
 vdi/hip_memory.cpp                       | 46 ++++++++++++++++++++++++
 4 files changed, 71 insertions(+)

diff --git a/include/hip/hcc_detail/hip_runtime_api.h b/include/hip/hcc_detail/hip_runtime_api.h
index d6b66090cd..d35d426a5e 100644
--- a/include/hip/hcc_detail/hip_runtime_api.h
+++ b/include/hip/hcc_detail/hip_runtime_api.h
@@ -3478,6 +3478,19 @@ hipError_t hipTexRefSetMipmappedArray(
     textureReference* texRef,
     hipMipmappedArray* mipmappedArray,
     unsigned int Flags);
+
+hipError_t hipMipmappedArrayCreate(
+    hipMipmappedArray_t* pHandle,
+    HIP_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc,
+    unsigned int numMipmapLevels);
+
+hipError_t hipMipmappedArrayDestroy(
+    hipMipmappedArray_t hMipmappedArray);
+
+hipError_t hipMipmappedArrayGetLevel(
+    hipArray_t* pLevelArray,
+    hipMipmappedArray_t hMipMappedArray,
+    unsigned int level);
 #endif
 
 /**
diff --git a/vdi/hip_hcc.def.in b/vdi/hip_hcc.def.in
index c6e4a00200..82d0283e1a 100644
--- a/vdi/hip_hcc.def.in
+++ b/vdi/hip_hcc.def.in
@@ -231,3 +231,9 @@ hiprtcGetProgramLogSize
 hiprtcGetCode
 hiprtcGetCodeSize
 hiprtcGetErrorString
+hipMipmappedArrayCreate
+hipMallocMipmappedArray
+hipMipmappedArrayDestroy
+hipFreeMipmappedArray
+hipMipmappedArrayGetLevel
+hipGetMipmappedArrayLevel
diff --git a/vdi/hip_hcc.map.in b/vdi/hip_hcc.map.in
index c26e79fc70..210789e420 100644
--- a/vdi/hip_hcc.map.in
+++ b/vdi/hip_hcc.map.in
@@ -225,6 +225,12 @@ global:
     hipTexRefSetMipmapLevelBias;
     hipTexRefSetMipmapLevelClamp;
     hipTexRefSetMipmappedArray;
+    hipMipmappedArrayCreate;
+    hipMallocMipmappedArray;
+    hipMipmappedArrayDestroy;
+    hipFreeMipmappedArray;
+    hipMipmappedArrayGetLevel;
+    hipGetMipmappedArrayLevel;
     extern "C++" {
     hip_impl::hipLaunchKernelGGLImpl*;
     hip_impl::demangle*;
diff --git a/vdi/hip_memory.cpp b/vdi/hip_memory.cpp
index fdcfa78ebc..718d907c9e 100644
--- a/vdi/hip_memory.cpp
+++ b/vdi/hip_memory.cpp
@@ -2055,3 +2055,49 @@ hipError_t hipMemcpyHtoAAsync(hipArray* dstArray,
 
   HIP_RETURN(ihipMemcpyHtoA(srcHost, dstArray, {0, 0, 0}, {dstOffset, 0, 0}, {ByteCount, 1, 1}, 0, 0, stream, true));
 }
+
+hipError_t hipMipmappedArrayCreate(hipMipmappedArray_t* pHandle,
+                                   HIP_ARRAY3D_DESCRIPTOR* pMipmappedArrayDesc,
+                                   unsigned int numMipmapLevels) {
+  HIP_INIT_API(hipMipmappedArrayCreate, pHandle, pMipmappedArrayDesc, numMipmapLevels);
+
+  HIP_RETURN(hipErrorNotSupported);
+}
+
+hipError_t hipMallocMipmappedArray(hipMipmappedArray_t *mipmappedArray,
+                                   const hipChannelFormatDesc* desc,
+                                   hipExtent extent,
+                                   unsigned int numLevels,
+                                   unsigned int flags) {
+  HIP_INIT_API(hipMallocMipmappedArray, mipmappedArray, desc, &extent, numLevels, flags);
+
+  HIP_RETURN(hipErrorNotSupported);
+}
+
+hipError_t hipMipmappedArrayDestroy(hipMipmappedArray_t hMipmappedArray) {
+  HIP_INIT_API(hipMipmappedArrayDestroy, hMipmappedArray);
+
+  HIP_RETURN(hipErrorNotSupported);
+}
+
+hipError_t hipFreeMipmappedArray(hipMipmappedArray_t mipmappedArray) {
+  HIP_INIT_API(hipFreeMipmappedArray, mipmappedArray);
+
+  HIP_RETURN(hipErrorNotSupported);
+}
+
+hipError_t hipMipmappedArrayGetLevel(hipArray_t* pLevelArray,
+                                     hipMipmappedArray_t hMipMappedArray,
+                                     unsigned int level) {
+  HIP_INIT_API(hipMipmappedArrayGetLevel, pLevelArray, hMipMappedArray, level);
+
+  HIP_RETURN(hipErrorNotSupported);
+}
+
+hipError_t hipGetMipmappedArrayLevel(hipArray_t *levelArray,
+                                     hipMipmappedArray_const_t mipmappedArray,
+                                     unsigned int level) {
+  HIP_INIT_API(hipGetMipmappedArrayLevel, levelArray, mipmappedArray, level);
+
+  HIP_RETURN(hipErrorNotSupported);
+}