Files
LBPM/gpu/Extras.cu

37 lines
1.0 KiB
Plaintext
Raw Normal View History

// Basic cuda functions callable from C/C++ code
#include <cuda.h>
#include <stdio.h>
extern "C" void ScaLBL_AllocateDeviceMemory(void** address, size_t size){
2015-06-25 16:18:45 -04:00
cudaMalloc(address,size);
cudaError_t err = cudaGetLastError();
if (cudaSuccess != err){
printf("Error in cudaMalloc: %s \n",cudaGetErrorString(err));
2015-06-25 16:18:45 -04:00
}
}
extern "C" void ScaLBL_FreeDeviceMemory(void* pointer){
cudaFree(pointer);
}
extern "C" void ScaLBL_CopyToDevice(void* dest, const void* source, size_t size){
cudaMemcpy(dest,source,size,cudaMemcpyHostToDevice);
2015-06-25 16:18:45 -04:00
cudaError_t err = cudaGetLastError();
if (cudaSuccess != err){
printf("Error in cudaMemcpy (host->device): %s \n",cudaGetErrorString(err));
2015-06-25 16:18:45 -04:00
}
}
extern "C" void ScaLBL_CopyToHost(void* dest, const void* source, size_t size){
cudaMemcpy(dest,source,size,cudaMemcpyDeviceToHost);
2015-06-25 16:18:45 -04:00
cudaError_t err = cudaGetLastError();
if (cudaSuccess != err){
printf("Error in cudaMemcpy (device->host): %s \n",cudaGetErrorString(err));
2015-06-25 16:18:45 -04:00
}
}
extern "C" void ScaLBL_DeviceBarrier(){
cudaDeviceSynchronize();
}