diff --git a/projects/hip/include/hip/hcc_detail/hip_runtime_api.h b/projects/hip/include/hip/hcc_detail/hip_runtime_api.h index d6b66090cd..d35d426a5e 100644 --- a/projects/hip/include/hip/hcc_detail/hip_runtime_api.h +++ b/projects/hip/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/projects/hip/vdi/hip_hcc.def.in b/projects/hip/vdi/hip_hcc.def.in index c6e4a00200..82d0283e1a 100644 --- a/projects/hip/vdi/hip_hcc.def.in +++ b/projects/hip/vdi/hip_hcc.def.in @@ -231,3 +231,9 @@ hiprtcGetProgramLogSize hiprtcGetCode hiprtcGetCodeSize hiprtcGetErrorString +hipMipmappedArrayCreate +hipMallocMipmappedArray +hipMipmappedArrayDestroy +hipFreeMipmappedArray +hipMipmappedArrayGetLevel +hipGetMipmappedArrayLevel diff --git a/projects/hip/vdi/hip_hcc.map.in b/projects/hip/vdi/hip_hcc.map.in index c26e79fc70..210789e420 100644 --- a/projects/hip/vdi/hip_hcc.map.in +++ b/projects/hip/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/projects/hip/vdi/hip_memory.cpp b/projects/hip/vdi/hip_memory.cpp index fdcfa78ebc..718d907c9e 100644 --- a/projects/hip/vdi/hip_memory.cpp +++ b/projects/hip/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); +}