diff --git a/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUAllocator.h b/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUAllocator.h new file mode 100644 index 000000000..015605775 --- /dev/null +++ b/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUAllocator.h @@ -0,0 +1,75 @@ +/* + + Copyright (C) DOLPHIN Project-Team, INRIA Lille - Nord Europe, 2006-2010 + + 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". + + 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. + + ParadisEO WebSite : http://paradiseo.gforge.inria.fr + Contact: paradiseo-help@lists.gforge.inria.fr + */ + +#ifndef __moGPUAllocator_H_ +#define __moGPUAllocator_H_ + +/** + * class for allocation data on GPU global memory + */ + +class moGPUAllocator { + +public: + + /** + * Constructor + */ + + moGPUAllocator() { + } + + /** + *Allocate data on GPU global memory + *@param _data the data to allocate on GPU global memory + *@param _dataSize the size of data to allocate on GPU memory + */ + template + void operator()(T* & _data, unsigned _dataSize) { + + //Allocate data in GPU memory + cudaMalloc((void**) &_data, _dataSize * sizeof(T)); + + } + + /** + * Destructor + */ + + ~moGPUAllocator() { + } + +}; + +#endif diff --git a/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUCopy.h b/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUCopy.h new file mode 100644 index 000000000..2d7c4b284 --- /dev/null +++ b/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUCopy.h @@ -0,0 +1,112 @@ +/* + + Copyright (C) DOLPHIN Project-Team, INRIA Lille - Nord Europe, 2006-2010 + + 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". + + 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. + + ParadisEO WebSite : http://paradiseo.gforge.inria.fr + Contact: paradiseo-help@lists.gforge.inria.fr + */ + +#ifndef __moGPUCopy_H_ +#define __moGPUCopy_H_ + +/** + * class to copy data from CPU memory to GPU global memory and vice versa + */ + +class moGPUCopy { + +public: + + /** + * Constructor + */ + + moGPUCopy() { + } + + /** + *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 + cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), + cudaMemcpyHostToDevice); + + } + + /** + *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 + cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), + cudaMemcpyHostToDevice); + } + + else { + //copy data from GPU global memory to GPU memory + cudaMemcpy(_data, _dataTocpy, _dataSize * sizeof(T), + cudaMemcpyDeviceToHost); + } + + } + + ~moGPUCopy() { + } + +}; +#endif diff --git a/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUDeallocator.h b/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUDeallocator.h new file mode 100644 index 000000000..18ef65d9c --- /dev/null +++ b/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUDeallocator.h @@ -0,0 +1,74 @@ +/* + + Copyright (C) DOLPHIN Project-Team, INRIA Lille - Nord Europe, 2006-2010 + + 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". + + 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. + + ParadisEO WebSite : http://paradiseo.gforge.inria.fr + Contact: paradiseo-help@lists.gforge.inria.fr + */ + +#ifndef __moGPUDeallocator_H_ +#define __moGPUDeallocator_H_ + +/** + * class for Disallocation of data from GPU global memory + */ + +class moGPUDeallocator { + +public: + + /** + * Constructor + */ + + moGPUDeallocator() { + } + + /** + *Deallocate data on GPU global memory + *@param _data the data to deallocate from GPU global memory + */ + template + void operator()(T* & _data) { + + //Deallocate data from GPU global memory + cudaFree(_data); + + } + + /** + * Destructor + */ + + ~moGPUDeallocator() { + } + +}; + +#endif diff --git a/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUObject.h b/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUObject.h new file mode 100644 index 000000000..74f2ccb7f --- /dev/null +++ b/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUObject.h @@ -0,0 +1,96 @@ +/* + + Copyright (C) DOLPHIN Project-Team, INRIA Lille - Nord Europe, 2006-2010 + + 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". + + 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. + + ParadisEO WebSite : http://paradiseo.gforge.inria.fr + Contact: paradiseo-help@lists.gforge.inria.fr + */ + +#ifndef __moGPUObject_H_ +#define __moGPUObject_H_ + +#include +#include +#include + +/** + * class of data managment on GPU global memory (allocation,desallocation & copy) + */ + +class moGPUObject { + +public: + + /* + * Constructor + */ + moGPUObject() { + + } + + /** + *Allocate & Copy data from CPU memory to GPU global memory (default copy) + *@param _data the data to allocate on GPU + *@param _dataTocpy the data to copy from CPU memory to _data on GPU memory + *@param _dataSize the size of data to copy + */ + template + void memCopy(T* & _data, T * & _dataTocpy, unsigned _dataSize) { + malloc(_data, _dataSize); + copy(_data, _dataTocpy, _dataSize); + } + + /** + *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 memCopyGlobalVariable(T* & _dev_data, T * & _dataTocpy) { + copy(_dev_data, _dataTocpy); + } + + /** + *Desallocate data on GPU global memory + *@param _data the data to desallocate from GPU global memory + */ + template + void memFree(T* & _data) { + free(_data); + } + +public: + + moGPUAllocator malloc; + moGPUCopy copy; + moGPUDeallocator free; + +}; + +#endif diff --git a/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUSpecificData.h b/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUSpecificData.h new file mode 100644 index 000000000..b3286dadc --- /dev/null +++ b/branches/ParadisEO-GPU/paradiseo-gpu/src/memory/moGPUSpecificData.h @@ -0,0 +1,85 @@ +/* + + Copyright (C) DOLPHIN Project-Team, INRIA Lille - Nord Europe, 2006-2010 + + 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". + + 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. + + ParadisEO WebSite : http://paradiseo.gforge.inria.fr + Contact: paradiseo-help@lists.gforge.inria.fr + */ + +#ifndef __moGPUSpecificData_H_ +#define __moGPUSpecificData_H_ + +#include + +/** + * class of managment of specific data problem + */ + +class moGPUSpecificData { + +public: + + /* + * Default constructor + */ + + moGPUSpecificData() { + sizeData = 0; + } + + /* + * Load data from file given in argument + * @param _file the name of data file + */ + + virtual void load(char* _file)=0; + + /* + * Return the size + * @return the size of data to load + */ + + virtual unsigned int getSize() { + return sizeData; + } + + /* + * Set the size of data to load + */ + + virtual void setSize(unsigned int _size) { + sizeData = _size; + } + +public: + unsigned int sizeData; + moGPUObject GPUObject; + +}; +#endif