diff --git a/hipamd/include/hip/amd_detail/hip_prof_str.h b/hipamd/include/hip/amd_detail/hip_prof_str.h index d0b24d01c0..b9d390ddd0 100644 --- a/hipamd/include/hip/amd_detail/hip_prof_str.h +++ b/hipamd/include/hip/amd_detail/hip_prof_str.h @@ -397,7 +397,6 @@ enum hip_api_id_t { HIP_API_ID_hipMemcpyFromArrayAsync = HIP_API_ID_NONE, HIP_API_ID_hipMemcpyHtoAAsync = HIP_API_ID_NONE, HIP_API_ID_hipMemcpyToArrayAsync = HIP_API_ID_NONE, - HIP_API_ID_hipModuleLaunchKernelExt = HIP_API_ID_NONE, HIP_API_ID_hipSetValidDevices = HIP_API_ID_NONE, HIP_API_ID_hipTexObjectCreate = HIP_API_ID_NONE, HIP_API_ID_hipTexObjectDestroy = HIP_API_ID_NONE, @@ -5477,8 +5476,6 @@ typedef struct hip_api_data_s { #define INIT_hipMemcpyHtoAAsync_CB_ARGS_DATA(cb_data) {}; // hipMemcpyToArrayAsync() #define INIT_hipMemcpyToArrayAsync_CB_ARGS_DATA(cb_data) {}; -// hipModuleLaunchKernelExt() -#define INIT_hipModuleLaunchKernelExt_CB_ARGS_DATA(cb_data) {}; // hipSetValidDevices() #define INIT_hipSetValidDevices_CB_ARGS_DATA(cb_data) {}; // hipTexObjectCreate() diff --git a/hipamd/src/amdhip.def b/hipamd/src/amdhip.def index ffaff7f57d..0b285d88ce 100644 --- a/hipamd/src/amdhip.def +++ b/hipamd/src/amdhip.def @@ -160,7 +160,6 @@ hipModuleGetFunction hipModuleGetGlobal hipModuleGetTexRef hipModuleLaunchKernel -hipModuleLaunchKernelExt hipModuleLaunchCooperativeKernel hipModuleLaunchCooperativeKernelMultiDevice hipLaunchCooperativeKernel diff --git a/hipamd/src/hip_hcc.map.in b/hipamd/src/hip_hcc.map.in index 204b139f2c..9494a3f44c 100644 --- a/hipamd/src/hip_hcc.map.in +++ b/hipamd/src/hip_hcc.map.in @@ -138,7 +138,6 @@ global: hipModuleGetGlobal; hipModuleGetTexRef; hipModuleLaunchKernel; - hipModuleLaunchKernelExt; hipLaunchCooperativeKernel; hipLaunchCooperativeKernelMultiDevice; hipModuleLoad; diff --git a/hipamd/src/hip_module.cpp b/hipamd/src/hip_module.cpp index 755a5594e2..8743beb2a8 100644 --- a/hipamd/src/hip_module.cpp +++ b/hipamd/src/hip_module.cpp @@ -498,20 +498,6 @@ hipError_t hipHccModuleLaunchKernel(hipFunction_t f, uint32_t globalWorkSizeX, extra, startEvent, stopEvent)); } -hipError_t hipModuleLaunchKernelExt(hipFunction_t f, uint32_t globalWorkSizeX, - uint32_t globalWorkSizeY, uint32_t globalWorkSizeZ, - uint32_t blockDimX, uint32_t blockDimY, uint32_t blockDimZ, - size_t sharedMemBytes, hipStream_t hStream, void** kernelParams, - void** extra, hipEvent_t startEvent, hipEvent_t stopEvent) { - HIP_INIT_API(hipModuleLaunchKernelExt, f, globalWorkSizeX, globalWorkSizeY, globalWorkSizeZ, - blockDimX, blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams, extra, - startEvent, stopEvent); - - HIP_RETURN(ihipModuleLaunchKernel(f, globalWorkSizeX, globalWorkSizeY, globalWorkSizeZ, blockDimX, - blockDimY, blockDimZ, sharedMemBytes, hStream, kernelParams, - extra, startEvent, stopEvent)); -} - hipError_t hipModuleLaunchCooperativeKernel(hipFunction_t f, unsigned int gridDimX, unsigned int gridDimY, unsigned int gridDimZ, unsigned int blockDimX, unsigned int blockDimY,