From dfc60a83597c054980493569c09692f71f9e5eed Mon Sep 17 00:00:00 2001
From: Aditya Atluri <Aditya.Atluri@amd.com>
Date: Mon, 29 Aug 2016 15:20:09 -0500
Subject: [PATCH] added hipInit for cuInit nvcc path

Change-Id: I594d08d936ac5d06f16e42c63062ac5776b65a0c
---
 include/nvcc_detail/hip_runtime_api.h | 11 +++++++++++
 tests/src/sampleModule.cpp            |  2 +-
 2 files changed, 12 insertions(+), 1 deletion(-)

diff --git a/include/nvcc_detail/hip_runtime_api.h b/include/nvcc_detail/hip_runtime_api.h
index d7f5d521a4..9ca3542569 100644
--- a/include/nvcc_detail/hip_runtime_api.h
+++ b/include/nvcc_detail/hip_runtime_api.h
@@ -148,6 +148,11 @@ default:
 }
 }
 
+inline static hipError_t hipInit(unsigned int flags)
+{
+    return hipCUResultTohipError(cuInit(flags));
+}
+
 inline static hipError_t hipDeviceReset() {
     return hipCUDAErrorTohipError(cudaDeviceReset());
 }
@@ -219,6 +224,12 @@ inline static hipError_t hipMemcpyDtoH(void* dst,
     return hipCUResultTohipError(cuMemcpyDtoH(dst, src, size));
 }
 
+inline static hipError_t hipMemcpyDtoD(hipDeviceptr_t dst,
+            hipDeviceptr_t src, size_t size)
+{
+    return hipCUResultTohipError(cuMemcpyDtoD(dst, src, size));
+}
+
 inline static hipError_t hipMemcpy(void* dst, const void* src, size_t sizeBytes, hipMemcpyKind copyKind) {
   return hipCUDAErrorTohipError(cudaMemcpy(dst, src, sizeBytes, hipMemcpyKindToCudaMemcpyKind(copyKind)));
 }
diff --git a/tests/src/sampleModule.cpp b/tests/src/sampleModule.cpp
index bef7345b4f..606b19717d 100644
--- a/tests/src/sampleModule.cpp
+++ b/tests/src/sampleModule.cpp
@@ -50,7 +50,7 @@ int main(){
 
 
 #ifdef __HIP_PLATFORM_NVCC__
-  	cuInit(0);
+  	hipInit(0);
 	  hipDevice_t device;
 	  hipCtx_t context;
 	  hipDeviceGet(&device, 0);