From ad3b9c1daba7045db5877a44cec40560131a43a6 Mon Sep 17 00:00:00 2001 From: boufaras Date: Thu, 10 Feb 2011 13:47:46 +0000 Subject: [PATCH] git-svn-id: svn://scm.gforge.inria.fr/svnroot/paradiseo@2140 331e1502-861f-0410-8da2-ba01fb791d7f --- ParadisEO-GPU/src/memory/moCudaCopy.h | 173 +++++++++++++------------- 1 file changed, 86 insertions(+), 87 deletions(-) diff --git a/ParadisEO-GPU/src/memory/moCudaCopy.h b/ParadisEO-GPU/src/memory/moCudaCopy.h index 9fd68e584..f38a0096c 100644 --- a/ParadisEO-GPU/src/memory/moCudaCopy.h +++ b/ParadisEO-GPU/src/memory/moCudaCopy.h @@ -1,36 +1,36 @@ /* - - Copyright (C) DOLPHIN Project-Team, INRIA Lille - Nord Europe, 2006-2010 + + Copyright (C) DOLPHIN Project-Team, INRIA Lille - Nord Europe, 2006-2010 - Boufaras Karima, Thé Van Luong + Boufaras Karima, Thé Van Luong - This software is governed by the CeCILL license under French law and - abiding by the rules of distribution of free software. You can use, - modify and/ or redistribute the software under the terms of the CeCILL - license as circulated by CEA, CNRS and INRIA at the following URL - "http://www.cecill.info". + This software is governed by the CeCILL license under French law and + abiding by the rules of distribution of free software. You can use, + modify and/ or redistribute the software under the terms of the CeCILL + license as circulated by CEA, CNRS and INRIA at the following URL + "http://www.cecill.info". - As a counterpart to the access to the source code and rights to copy, - modify and redistribute granted by the license, users are provided only - with a limited warranty and the software's author, the holder of the - economic rights, and the successive licensors have only limited liability. + As a counterpart to the access to the source code and rights to copy, + modify and redistribute granted by the license, users are provided only + with a limited warranty and the software's author, the holder of the + economic rights, and the successive licensors have only limited liability. - In this respect, the user's attention is drawn to the risks associated - with loading, using, modifying and/or developing or reproducing the - software by the user in light of its specific status of free software, - that may mean that it is complicated to manipulate, and that also - therefore means that it is reserved for developers and experienced - professionals having in-depth computer knowledge. Users are therefore - encouraged to load and test the software's suitability as regards their - requirements in conditions enabling the security of their systems and/or - data to be ensured and, more generally, to use and operate it in the - same conditions as regards security. - The fact that you are presently reading this means that you have had - knowledge of the CeCILL license and that you accept its terms. + In this respect, the user's attention is drawn to the risks associated + with loading, using, modifying and/or developing or reproducing the + software by the user in light of its specific status of free software, + that may mean that it is complicated to manipulate, and that also + therefore means that it is reserved for developers and experienced + professionals having in-depth computer knowledge. Users are therefore + encouraged to load and test the software's suitability as regards their + requirements in conditions enabling the security of their systems and/or + data to be ensured and, more generally, to use and operate it in the + same conditions as regards security. + The fact that you are presently reading this means that you have had + knowledge of the CeCILL license and that you accept its terms. - ParadisEO WebSite : http://paradiseo.gforge.inria.fr - Contact: paradiseo-help@lists.gforge.inria.fr - */ + ParadisEO WebSite : http://paradiseo.gforge.inria.fr + Contact: paradiseo-help@lists.gforge.inria.fr +*/ #ifndef _moCudaCopy_H_ #define _moCudaCopy_H_ @@ -46,73 +46,72 @@ class moCudaCopy { public: - /** - * Constructor - */ + /** + * Constructor + */ - moCudaCopy() { - } + moCudaCopy() { + } - /** - *Copy data from CPU memory to GPU global memory (default copy) - *@param _data the data representation where the data will be copied - *@param _dataTocpy the data to copy from CPU memory to GPU memory - *@param _dataSize the size of data to copy - */ - template - void operator()(T* & _data, T * & _dataTocpy, unsigned _dataSize) { + /** + *Copy data from CPU memory to GPU global memory (default copy) + *@param _data the data representation where the data will be copied + *@param _dataTocpy the data to copy from CPU memory to GPU memory + *@param _dataSize the size of data to copy + */ + template + void operator()(T* & _data, T * & _dataTocpy, unsigned _dataSize) { - //copy data from CPU memory to GPU memory - CUDA_SAFE_CALL(cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), + //copy data from CPU memory to GPU memory + CUDA_SAFE_CALL(cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), + cudaMemcpyHostToDevice)); + + // Check if the copy of data is failed + CUT_CHECK_ERROR("Copy of data from CPU to GPU global memory failed"); + } + + /** + *Copy device data from GPU global memory to global variable declared in device + *@param _dev_data the device global variable + *@param _dataTocpy the data to copy GPU global memory to GPU global variable + */ + template + void operator()(T* & _dev_data, T * & _dataTocpy) { + + //Copy n bytes from the memory area pointed to by _dataTocpy to the memory area pointed to by offset bytes from the start of symbol _dev_data + + cudaMemcpyToSymbol(_dev_data, &_dataTocpy, sizeof(_dataTocpy)); + + } + + /** + *Copy data from CPU memory to GPU global memory and vice versa + *@param _data the data representation where the data will be copied + *@param _dataTocpy the data to copy from CPU memory to GPU memory and vice versa + *@param _dataSize the size of data to copy + *@param _HostToDevice the direction of copy(true if copy will be done from CPU memory to GPU memory) + */ + template + void operator()(T* & _data, T * & _dataTocpy, unsigned _dataSize, + bool _HostToDevice) { + + if (_HostToDevice) { + + //copy data from CPU memory to GPU global memory + CUDA_SAFE_CALL(cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), cudaMemcpyHostToDevice)); + } - // Check if the copy of data is failed - CUT_CHECK_ERROR("Copy of data from CPU to GPU global memory failed"); + else { + //copy data from GPU global memory to GPU memory + CUDA_SAFE_CALL(cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), + cudaMemcpyDeviceToHost)); + } - } + } - /** - *Copy device data from GPU global memory to global variable declared in device - *@param _dev_data the device global variable - *@param _dataTocpy the data to copy GPU global memory to GPU global variable - */ - template - void operator()(T* & _dev_data, T * & _dataTocpy) { - - //Copy n bytes from the memory area pointed to by _dataTocpy to the memory area pointed to by offset bytes from the start of symbol _dev_data - - cudaMemcpyToSymbol(_dev_data, &_dataTocpy, sizeof(_dataTocpy)); - - } - - /** - *Copy data from CPU memory to GPU global memory and vice versa - *@param _data the data representation where the data will be copied - *@param _dataTocpy the data to copy from CPU memory to GPU memory and vice versa - *@param _dataSize the size of data to copy - *@param _HostToDevice the direction of copy(true if copy will be done from CPU memory to GPU memory) - */ - template - void operator()(T* & _data, T * & _dataTocpy, unsigned _dataSize, - bool _HostToDevice) { - - if (_HostToDevice) { - - //copy data from CPU memory to GPU global memory - CUDA_SAFE_CALL(cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), - cudaMemcpyHostToDevice)); - } - - else { - //copy data from GPU global memory to GPU memory - CUDA_SAFE_CALL(cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), - cudaMemcpyDeviceToHost)); - } - - } - - ~moCudaCopy() { - } + ~moCudaCopy() { + } }; #endif