nojhan/paradiseo
1
0
Fork 0
Code Issues Pull requests Projects Releases Packages Wiki Activity

independant from cutil.h

Browse source 
git-svn-id: svn://scm.gforge.inria.fr/svnroot/paradiseo@2463 331e1502-861f-0410-8da2-ba01fb791d7f
This commit is contained in:
boufaras 2011-09-29 15:31:03 +00:00
commit 860bac76d3
1 changed files with 6 additions and 11 deletions
Download patch file Download diff file Expand all files Collapse all files

17
branches/ParadisEO-GPU/src/memory/moGPUCopy.h
View file

@ -35,9 +35,6 @@
#ifndef __moGPUCopy_H_ #ifndef __moGPUCopy_H_
#define __moGPUCopy_H_ #define __moGPUCopy_H_
// CUDA includes
#include <cutil.h>
/** /**
* class to copy data from CPU memory to GPU global memory and vice versa * class to copy data from CPU memory to GPU global memory and vice versa
*/ */
@ -63,11 +60,9 @@ public:
void operator()(T* & _data, T * & _dataTocpy, unsigned _dataSize) { void operator()(T* & _data, T * & _dataTocpy, unsigned _dataSize) {
//copy data from CPU memory to GPU memory //copy data from CPU memory to GPU memory
CUDA_SAFE_CALL(cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T),
cudaMemcpyHostToDevice)); cudaMemcpyHostToDevice);
// Check if the copy of data is failed
CUT_CHECK_ERROR("Copy of data from CPU to GPU global memory failed");
} }
/** /**
@ -98,14 +93,14 @@ public:
if (_HostToDevice) { if (_HostToDevice) {
//copy data from CPU memory to GPU global memory //copy data from CPU memory to GPU global memory
CUDA_SAFE_CALL(cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T),
cudaMemcpyHostToDevice)); cudaMemcpyHostToDevice);
} }
else { else {
//copy data from GPU global memory to GPU memory //copy data from GPU global memory to GPU memory
CUDA_SAFE_CALL(cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T),
cudaMemcpyDeviceToHost)); cudaMemcpyDeviceToHost);
} }
} }