diff --git a/projects/clr/rocclr/device/rocm/rocmemory.cpp b/projects/clr/rocclr/device/rocm/rocmemory.cpp index 6113262340..6ab08b00a9 100644 --- a/projects/clr/rocclr/device/rocm/rocmemory.cpp +++ b/projects/clr/rocclr/device/rocm/rocmemory.cpp @@ -615,7 +615,7 @@ Buffer::Buffer(const roc::Device& dev, size_t size) : roc::Memory(dev, size) {} Buffer::~Buffer() { if (owner() == nullptr) { - dev().memFree(deviceMemory_, size()); + dev().hostFree(deviceMemory_, size()); } else { destroy(); @@ -663,7 +663,7 @@ void Buffer::destroy() { ClPrint(amd::LOG_DEBUG, amd::LOG_MEM, "[ROCClr] munmap failed \n"); } } else { - dev().memFree(deviceMemory_, size()); + dev().hostFree(deviceMemory_, size()); } } else if (memFlags & ROCCLR_MEM_HSA_SIGNAL_MEMORY) { if (HSA_STATUS_SUCCESS != hsa_signal_destroy(signal_)) { @@ -672,7 +672,7 @@ void Buffer::destroy() { } deviceMemory_ = nullptr; } else { - dev().memFree(deviceMemory_, size()); + dev().hostFree(deviceMemory_, size()); } } else { dev().memFree(deviceMemory_, size()); diff --git a/projects/clr/rocclr/platform/runtime.cpp b/projects/clr/rocclr/platform/runtime.cpp index 6072a62a9b..7f80919c46 100644 --- a/projects/clr/rocclr/platform/runtime.cpp +++ b/projects/clr/rocclr/platform/runtime.cpp @@ -120,12 +120,4 @@ uint ReferenceCountedObject::release() { return newCount; } -#ifndef _WIN32 -void __attribute__((destructor)) hipTearDown() { - if (amd::IS_HIP) { - Runtime::tearDown(); - } -} -#endif - } // namespace amd