From fd7a8f036731193f5ff4c5cff39fa7cbf9db1d57 Mon Sep 17 00:00:00 2001
From: Vladislav Sytchenko <vladislav.sytchenko@amd.com>
Date: Fri, 27 Mar 2020 14:02:46 -0400
Subject: [PATCH] (SWDEV-228794)

Add hipMallocHost()

Change-Id: Ia3c7c5ca94b39fe30f3a51d1b60782d3472259ff
---
 vdi/hip_hcc.def.in |  1 +
 vdi/hip_hcc.map.in |  1 +
 vdi/hip_memory.cpp | 11 +++++++++++
 3 files changed, 13 insertions(+)

diff --git a/vdi/hip_hcc.def.in b/vdi/hip_hcc.def.in
index 82d0283e1a..6bf962a084 100644
--- a/vdi/hip_hcc.def.in
+++ b/vdi/hip_hcc.def.in
@@ -237,3 +237,4 @@ hipMipmappedArrayDestroy
 hipFreeMipmappedArray
 hipMipmappedArrayGetLevel
 hipGetMipmappedArrayLevel
+hipMallocHost
diff --git a/vdi/hip_hcc.map.in b/vdi/hip_hcc.map.in
index 210789e420..ec1c8a4558 100644
--- a/vdi/hip_hcc.map.in
+++ b/vdi/hip_hcc.map.in
@@ -231,6 +231,7 @@ global:
     hipFreeMipmappedArray;
     hipMipmappedArrayGetLevel;
     hipGetMipmappedArrayLevel;
+    hipMallocHost;
     extern "C++" {
     hip_impl::hipLaunchKernelGGLImpl*;
     hip_impl::demangle*;
diff --git a/vdi/hip_memory.cpp b/vdi/hip_memory.cpp
index 80710e0d13..467f996952 100644
--- a/vdi/hip_memory.cpp
+++ b/vdi/hip_memory.cpp
@@ -2101,3 +2101,14 @@ hipError_t hipGetMipmappedArrayLevel(hipArray_t *levelArray,
 
   HIP_RETURN(hipErrorNotSupported);
 }
+
+hipError_t hipMallocHost(void** ptr,
+                         size_t size) {
+  HIP_INIT_API(hipMallocHost, ptr, size);
+
+  if (ptr == nullptr) {
+    HIP_RETURN(hipErrorInvalidValue);
+  }
+
+  HIP_RETURN(ihipMalloc(ptr, size, CL_MEM_SVM_FINE_GRAIN_BUFFER));
+}
\ No newline at end of file