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

git-svn-id: svn://scm.gforge.inria.fr/svnroot/paradiseo@2138 331e1502-861f-0410-8da2-ba01fb791d7f

Browse source
This commit is contained in:
boufaras 2011-02-10 13:44:47 +00:00
commit c548ca9e17
1 changed files with 120 additions and 120 deletions
Download patch file Download diff file Expand all files Collapse all files

190
ParadisEO-GPU/src/eval/moCudaEval.h
View file

@ -1,36 +1,36 @@
/* /*
<moCudaEval.h> <moCudaEval.h>
Copyright (C) DOLPHIN Project-Team, INRIA Lille - Nord Europe, 2006-2010 Copyright (C) DOLPHIN Project-Team, INRIA Lille - Nord Europe, 2006-2010
Karima Boufaras, Thé Van LUONG Karima Boufaras, Thé Van LUONG
This software is governed by the CeCILL license under French law and This software is governed by the CeCILL license under French law and
abiding by the rules of distribution of free software. You can use, abiding by the rules of distribution of free software. You can use,
modify and/ or redistribute the software under the terms of the CeCILL modify and/ or redistribute the software under the terms of the CeCILL
license as circulated by CEA, CNRS and INRIA at the following URL license as circulated by CEA, CNRS and INRIA at the following URL
"http://www.cecill.info". "http://www.cecill.info".
As a counterpart to the access to the source code and rights to copy, 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 modify and redistribute granted by the license, users are provided only
with a limited warranty and the software's author, the holder of the with a limited warranty and the software's author, the holder of the
economic rights, and the successive licensors have only limited liability. economic rights, and the successive licensors have only limited liability.
In this respect, the user's attention is drawn to the risks associated In this respect, the user's attention is drawn to the risks associated
with loading, using, modifying and/or developing or reproducing the with loading, using, modifying and/or developing or reproducing the
software by the user in light of its specific status of free software, 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 that may mean that it is complicated to manipulate, and that also
therefore means that it is reserved for developers and experienced therefore means that it is reserved for developers and experienced
professionals having in-depth computer knowledge. Users are therefore professionals having in-depth computer knowledge. Users are therefore
encouraged to load and test the software's suitability as regards their encouraged to load and test the software's suitability as regards their
requirements in conditions enabling the security of their systems and/or 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 data to be ensured and, more generally, to use and operate it in the
same conditions as regards security. same conditions as regards security.
The fact that you are presently reading this means that you have had The fact that you are presently reading this means that you have had
knowledge of the CeCILL license and that you accept its terms. knowledge of the CeCILL license and that you accept its terms.
ParadisEO WebSite : http://paradiseo.gforge.inria.fr ParadisEO WebSite : http://paradiseo.gforge.inria.fr
Contact: paradiseo-help@lists.gforge.inria.fr Contact: paradiseo-help@lists.gforge.inria.fr
*/ */
#ifndef moCudaEval_H #ifndef moCudaEval_H
#define moCudaEval_H #define moCudaEval_H
@ -42,94 +42,94 @@
template<class Neighbor> template<class Neighbor>
class moCudaEval: public moEval<Neighbor> { class moCudaEval: public moEval<Neighbor> {
public: public:
/** /**
* Define type of a solution corresponding to Neighbor * Define type of a solution corresponding to Neighbor
*/ */
typedef typename Neighbor::EOT EOT; typedef typename Neighbor::EOT EOT;
typedef typename EOT::Fitness Fitness; typedef typename EOT::Fitness Fitness;
/** /**
* Constructor * Constructor
* @param _neighborhoodSize the size of the neighborhood * @param _neighborhoodSize the size of the neighborhood
*/ */
moCudaEval(unsigned int _neighborhoodSize) { moCudaEval(unsigned int _neighborhoodSize) {
neighborhoodSize = _neighborhoodSize; neighborhoodSize = _neighborhoodSize;
host_FitnessArray = new Fitness[neighborhoodSize]; host_FitnessArray = new Fitness[neighborhoodSize];
cudaMalloc((void**) &device_FitnessArray, neighborhoodSize cudaMalloc((void**) &device_FitnessArray, neighborhoodSize
* sizeof(Fitness)); * sizeof(Fitness));
kernel_Dim = neighborhoodSize / BLOCK_SIZE + ((neighborhoodSize kernel_Dim = neighborhoodSize / BLOCK_SIZE + ((neighborhoodSize
% BLOCK_SIZE == 0) ? 0 : 1); % BLOCK_SIZE == 0) ? 0 : 1);
} }
/** /**
* Destructor * Destructor
*/ */
~moCudaEval() { ~moCudaEval() {
delete[] host_FitnessArray; delete[] host_FitnessArray;
cudaFree(device_FitnessArray); cudaFree(device_FitnessArray);
cudaFree(&device_solution); cudaFree(&device_solution);
} }
/** /**
* Set fitness of a solution neighbors * Set fitness of a solution neighbors
*@param _sol the solution which generate the neighborhood *@param _sol the solution which generate the neighborhood
*@param _neighbor the current neighbor *@param _neighbor the current neighbor
*/ */
void operator()(EOT & _sol, Neighbor & _neighbor) { void operator()(EOT & _sol, Neighbor & _neighbor) {
_neighbor.fitness(host_FitnessArray[_neighbor.index()]); _neighbor.fitness(host_FitnessArray[_neighbor.index()]);
} }
/** /**
* Compute fitness for all Kswap solution neighbors in device * Compute fitness for all Kswap solution neighbors in device
* @param _sol the solution which generate the neighborhood * @param _sol the solution which generate the neighborhood
* @param _mapping the neighborhood mapping * @param _mapping the neighborhood mapping
* @param _Kswap the number of swap * @param _Kswap the number of swap
*/ */
virtual void neighborhoodKswapEval(EOT & _sol, unsigned * _mapping, virtual void neighborhoodKswapEval(EOT & _sol, unsigned * _mapping,
unsigned _Kswap) { unsigned _Kswap) {
} }
/** /**
* Compute fitness for all Kflip solution neighbors in device * Compute fitness for all Kflip solution neighbors in device
* @param _sol the solution which generate the neighborhood * @param _sol the solution which generate the neighborhood
* @param _mapping the neighborhood mapping * @param _mapping the neighborhood mapping
* @param _Kflip the number of bit to flip * @param _Kflip the number of bit to flip
*/ */
virtual void neighborhoodKflipEval(EOT & _sol, unsigned * _mapping, virtual void neighborhoodKflipEval(EOT & _sol, unsigned * _mapping,
unsigned _Kflip) { unsigned _Kflip) {
} }
/** /**
* Compute fitness for all solution neighbors in device * Compute fitness for all solution neighbors in device
* @param _sol the solution which generate the neighborhood * @param _sol the solution which generate the neighborhood
*/ */
virtual void neighborhoodEval(EOT & _sol)=0; virtual void neighborhoodEval(EOT & _sol)=0;
protected: protected:
//the host array to save all neighbors fitness //the host array to save all neighbors fitness
Fitness * host_FitnessArray; Fitness * host_FitnessArray;
//the device array to save neighbors fitness computed in device //the device array to save neighbors fitness computed in device
Fitness * device_FitnessArray; Fitness * device_FitnessArray;
//the device solution //the device solution
EOT device_solution; EOT device_solution;
//the size of neighborhood //the size of neighborhood
unsigned int neighborhoodSize; unsigned int neighborhoodSize;
//Cuda kernel dimension //Cuda kernel dimension
int kernel_Dim; int kernel_Dim;
}; };