Updates to GPU memory allocation to align with P2P paper

Author: bo3z

sw/CMakeLists.txt

@@ -152,7 +152,7 @@ if(EN_GPU)
     )
 
     # Add GPU libraries
-    target_link_libraries(Coyote PUBLIC hip::device numa pthread drm drm_amdgpu rt dl hsa-runtime64 hsakmt)
+    target_link_libraries(Coyote PUBLIC hip::device numa pthread drm drm_amdgpu rt dl hsa-runtime64 hsakmt rocm_smi64)
 endif()
 
 ##############################

sw/include/coyote/cGpu.hpp

@@ -34,6 +34,7 @@
 #include <stdexcept>
 
 #include <hsa.h>
+#include <hip/hip_runtime.h>
 #include <hsa/hsa_ext_amd.h>
 
 namespace coyote {

sw/src/cThread.cpp

@@ -486,9 +486,8 @@ void* cThread::getMem(CoyoteAlloc&& alloc) {
                 #endif 
 
                 // Allocate the GPU memory
-                err = hsa_memory_allocate(*info_params.region, alloc.size, (void **) &(mem)); 
-                if (err != HSA_STATUS_SUCCESS) {
-                    std::cerr << "ERROR: cThread::getMem() - Failed to allocate GPU memory!" << std::endl;;
+                if (hipMalloc((void **) &mem, alloc.size)) {
+                    std::cerr << "ERROR: cThread::getMem() - hipMalloc failed to allocate GPU memory!" << std::endl;;
                     return nullptr;
                 }