2014-03-17 10:14:46 -04:00
|
|
|
// Basic cuda functions callable from C/C++ code
|
|
|
|
|
#include <cuda.h>
|
|
|
|
|
|
2014-03-19 09:07:50 -04:00
|
|
|
extern "C" void AllocateDeviceMemory(void** address, size_t size){
|
2015-06-25 16:18:45 -04:00
|
|
|
cudaMalloc(address,size);
|
|
|
|
|
cudaError_t err = cudaGetLastError();
|
|
|
|
|
if (cudaSuccess != err){
|
2015-06-25 17:44:13 -04:00
|
|
|
printf("Error in cudaMalloc: %s \n",cudaGetErrorString(err));
|
2015-06-25 16:18:45 -04:00
|
|
|
}
|
2014-03-17 10:14:46 -04:00
|
|
|
}
|
|
|
|
|
|
2014-03-19 09:07:50 -04:00
|
|
|
extern "C" void CopyToDevice(void* dest, void* source, size_t size){
|
2014-03-17 10:14:46 -04:00
|
|
|
cudaMemcpy(dest,source,size,cudaMemcpyHostToDevice);
|
2015-06-25 16:18:45 -04:00
|
|
|
cudaError_t err = cudaGetLastError();
|
|
|
|
|
if (cudaSuccess != err){
|
2015-06-25 17:44:13 -04:00
|
|
|
printf("Error in cudaMemcpy (host->device): %s \n",cudaGetErrorString(err));
|
2015-06-25 16:18:45 -04:00
|
|
|
}
|
2014-03-17 10:14:46 -04:00
|
|
|
}
|
|
|
|
|
|
|
|
|
|
|
2014-03-19 09:07:50 -04:00
|
|
|
extern "C" void CopyToHost(void* dest, void* source, size_t size){
|
2014-03-17 10:14:46 -04:00
|
|
|
cudaMemcpy(dest,source,size,cudaMemcpyDeviceToHost);
|
2015-06-25 16:18:45 -04:00
|
|
|
cudaError_t err = cudaGetLastError();
|
|
|
|
|
if (cudaSuccess != err){
|
2015-06-25 17:44:13 -04:00
|
|
|
printf("Error in cudaMemcpy (device->host): %s \n",cudaGetErrorString(err));
|
2015-06-25 16:18:45 -04:00
|
|
|
}
|
2014-03-17 10:14:46 -04:00
|
|
|
}
|
|
|
|
|
|
2014-03-19 09:07:50 -04:00
|
|
|
extern "C" void DeviceBarrier(){
|
2014-03-17 10:14:46 -04:00
|
|
|
cudaDeviceSynchronize();
|
|
|
|
|
}
|