From e9bc4034d8ba2c17f2ca1bafcd277eced7780bc1 Mon Sep 17 00:00:00 2001 From: Yaxun Sam Liu Date: Tue, 19 Mar 2019 11:11:49 -0400 Subject: [PATCH] Add declaration of symbol related API for VDI --- include/hip/hcc_detail/hip_runtime_api.h | 21 ++++++++++++++++++++- 1 file changed, 20 insertions(+), 1 deletion(-) diff --git a/include/hip/hcc_detail/hip_runtime_api.h b/include/hip/hcc_detail/hip_runtime_api.h index ea93d28bfe..7d227f2fac 100644 --- a/include/hip/hcc_detail/hip_runtime_api.h +++ b/include/hip/hcc_detail/hip_runtime_api.h @@ -1377,7 +1377,26 @@ hipError_t hipMemcpyDtoHAsync(void* dst, hipDeviceptr_t src, size_t sizeBytes, h hipError_t hipMemcpyDtoDAsync(hipDeviceptr_t dst, hipDeviceptr_t src, size_t sizeBytes, hipStream_t stream); -#if !__HIP_VDI__ +#if __HIP_VDI__ +hipError_t hipModuleGetGlobal(hipDeviceptr_t* dptr, size_t* bytes, + hipModule_t hmod, const char* name); + +hipError_t hipGetSymbolAddress(void** devPtr, const void* symbolName); +hipError_t hipGetSymbolSize(size_t* size, const void* symbolName); +hipError_t hipMemcpyToSymbol(const void* symbolName, const void* src, + size_t sizeBytes, size_t offset __dparm(0), + hipMemcpyKind kind __dparm(hipMemcpyHostToDevice)); +hipError_t hipMemcpyToSymbolAsync(const void* symbolName, const void* src, + size_t sizeBytes, size_t offset, + hipMemcpyKind kind, hipStream_t stream __dparm(0)); +hipError_t hipMemcpyFromSymbol(void* dst, const void* symbolName, + size_t sizeBytes, size_t offset __dparm(0), + hipMemcpyKind kind __dparm(hipMemcpyDeviceToHost)); +hipError_t hipMemcpyFromSymbolAsync(void* dst, const void* symbolName, + size_t sizeBytes, size_t offset, + hipMemcpyKind kind, + hipStream_t stream __dparm(0)); +#else __attribute__((visibility("hidden"))) hipError_t hipModuleGetGlobal(void**, size_t*, hipModule_t, const char*);