From 2408d0cf7955a659558a39545aac7d3cf4a880d2 Mon Sep 17 00:00:00 2001 From: Ben Sander Date: Wed, 7 Jun 2017 09:05:30 -0500 Subject: [PATCH] Use amHostCoherentFlag. Requires new HCC version. [ROCm/clr commit: 9bfc7b0e139c8f84b6d29316b84f65250a077b9b] --- projects/clr/hipamd/src/hip_memory.cpp | 5 +++-- 1 file changed, 3 insertions(+), 2 deletions(-) diff --git a/projects/clr/hipamd/src/hip_memory.cpp b/projects/clr/hipamd/src/hip_memory.cpp index 3ab7713afa..c04c2611c3 100644 --- a/projects/clr/hipamd/src/hip_memory.cpp +++ b/projects/clr/hipamd/src/hip_memory.cpp @@ -243,6 +243,7 @@ hipError_t hipMalloc(void** ptr, size_t sizeBytes) } + hipError_t hipHostMalloc(void** ptr, size_t sizeBytes, unsigned int flags) { HIP_INIT_SPECIAL_API((TRACE_MEM), ptr, sizeBytes, flags); @@ -289,10 +290,10 @@ hipError_t hipHostMalloc(void** ptr, size_t sizeBytes, unsigned int flags) if (flags & hipHostMallocCoherent) { amFlags = amHostCoherent; } else if (flags & hipHostMallocNonCoherent) { - amFlags = amHostPinned; + amFlags = amHostNonCoherent; } else { // depends on env variables: - amFlags = HIP_COHERENT_HOST_ALLOC ? amHostCoherent : amHostPinned; + amFlags = HIP_COHERENT_HOST_ALLOC ? amHostCoherent : amHostNonCoherent; }