From c548ca9e170413f11c06f89da584aa275727b86b Mon Sep 17 00:00:00 2001 From: boufaras Date: Thu, 10 Feb 2011 13:44:47 +0000 Subject: [PATCH] git-svn-id: svn://scm.gforge.inria.fr/svnroot/paradiseo@2138 331e1502-861f-0410-8da2-ba01fb791d7f --- ParadisEO-GPU/src/eval/moCudaEval.h | 190 ++++++++++++++-------------- 1 file changed, 95 insertions(+), 95 deletions(-) diff --git a/ParadisEO-GPU/src/eval/moCudaEval.h b/ParadisEO-GPU/src/eval/moCudaEval.h index 98c92a7a4..cc780a113 100644 --- a/ParadisEO-GPU/src/eval/moCudaEval.h +++ b/ParadisEO-GPU/src/eval/moCudaEval.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 - Karima Boufaras, Thé Van LUONG + Karima Boufaras, 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 moCudaEval_H #define moCudaEval_H @@ -42,94 +42,94 @@ template class moCudaEval: public moEval { -public: + public: - /** - * Define type of a solution corresponding to Neighbor - */ - typedef typename Neighbor::EOT EOT; + /** + * Define type of a solution corresponding to Neighbor + */ + typedef typename Neighbor::EOT EOT; - typedef typename EOT::Fitness Fitness; + typedef typename EOT::Fitness Fitness; - /** - * Constructor - * @param _neighborhoodSize the size of the neighborhood - */ + /** + * Constructor + * @param _neighborhoodSize the size of the neighborhood + */ - moCudaEval(unsigned int _neighborhoodSize) { + moCudaEval(unsigned int _neighborhoodSize) { - neighborhoodSize = _neighborhoodSize; - host_FitnessArray = new Fitness[neighborhoodSize]; - cudaMalloc((void**) &device_FitnessArray, neighborhoodSize - * sizeof(Fitness)); - kernel_Dim = neighborhoodSize / BLOCK_SIZE + ((neighborhoodSize - % BLOCK_SIZE == 0) ? 0 : 1); - } + neighborhoodSize = _neighborhoodSize; + host_FitnessArray = new Fitness[neighborhoodSize]; + cudaMalloc((void**) &device_FitnessArray, neighborhoodSize + * sizeof(Fitness)); + kernel_Dim = neighborhoodSize / BLOCK_SIZE + ((neighborhoodSize + % BLOCK_SIZE == 0) ? 0 : 1); + } - /** - * Destructor - */ + /** + * Destructor + */ - ~moCudaEval() { + ~moCudaEval() { - delete[] host_FitnessArray; - cudaFree(device_FitnessArray); - cudaFree(&device_solution); - } + delete[] host_FitnessArray; + cudaFree(device_FitnessArray); + cudaFree(&device_solution); + } - /** - * Set fitness of a solution neighbors - *@param _sol the solution which generate the neighborhood - *@param _neighbor the current neighbor - */ + /** + * Set fitness of a solution neighbors + *@param _sol the solution which generate the neighborhood + *@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 - * @param _sol the solution which generate the neighborhood - * @param _mapping the neighborhood mapping - * @param _Kswap the number of swap - */ - virtual void neighborhoodKswapEval(EOT & _sol, unsigned * _mapping, - unsigned _Kswap) { + /** + * Compute fitness for all Kswap solution neighbors in device + * @param _sol the solution which generate the neighborhood + * @param _mapping the neighborhood mapping + * @param _Kswap the number of swap + */ + virtual void neighborhoodKswapEval(EOT & _sol, unsigned * _mapping, + unsigned _Kswap) { - } + } - /** - * Compute fitness for all Kflip solution neighbors in device - * @param _sol the solution which generate the neighborhood - * @param _mapping the neighborhood mapping - * @param _Kflip the number of bit to flip - */ - virtual void neighborhoodKflipEval(EOT & _sol, unsigned * _mapping, - unsigned _Kflip) { + /** + * Compute fitness for all Kflip solution neighbors in device + * @param _sol the solution which generate the neighborhood + * @param _mapping the neighborhood mapping + * @param _Kflip the number of bit to flip + */ + virtual void neighborhoodKflipEval(EOT & _sol, unsigned * _mapping, + unsigned _Kflip) { - } + } - /** - * Compute fitness for all solution neighbors in device - * @param _sol the solution which generate the neighborhood - */ + /** + * Compute fitness for all solution neighbors in device + * @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 - Fitness * host_FitnessArray; - //the device array to save neighbors fitness computed in device - Fitness * device_FitnessArray; - //the device solution - EOT device_solution; - //the size of neighborhood - unsigned int neighborhoodSize; - //Cuda kernel dimension - int kernel_Dim; + //the host array to save all neighbors fitness + Fitness * host_FitnessArray; + //the device array to save neighbors fitness computed in device + Fitness * device_FitnessArray; + //the device solution + EOT device_solution; + //the size of neighborhood + unsigned int neighborhoodSize; + //Cuda kernel dimension + int kernel_Dim; };