Homec4science
Diffusion tamaas (features/netcdf-mpi) Browse

tamaas/src/gpu/unified_allocator.hh
30d402099764features/netcdf-mpi

Last Change
Raw File

unified_allocator.hh
View Options

/**
* @file
*
* @author Lucas Frérot <lucas.frerot@epfl.ch>
*
* @section LICENSE
*
* Copyright (©) 2017 EPFL (Ecole Polytechnique Fédérale de
* Lausanne) Laboratory (LSMS - Laboratoire de Simulation en Mécanique des
* Solides)
*
* Tamaas is free software: you can redistribute it and/or modify it under the
* terms of the GNU Lesser General Public License as published by the Free
* Software Foundation, either version 3 of the License, or (at your option) any
* later version.
*
* Tamaas is distributed in the hope that it will be useful, but WITHOUT ANY
* WARRANTY; without even the implied warranty of MERCHANTABILITY or FITNESS FOR
* A PARTICULAR PURPOSE. See the GNU Lesser General Public License for more
* details.
*
* You should have received a copy of the GNU Lesser General Public License
* along with Tamaas. If not, see <http://www.gnu.org/licenses/>.
*
*/
/* -------------------------------------------------------------------------- */
#ifndef __UNIFIED_ALLOCATOR_HH__
#define __UNIFIED_ALLOCATOR_HH__
/* -------------------------------------------------------------------------- */
#include <memory>
#include <cuda_runtime_api.h>
/* -------------------------------------------------------------------------- */
namespace tamaas {
/// Class allocating [unified memory](http://docs.nvidia.com/cuda/cuda-runtime-api/group__CUDART__MEMORY.html#group__CUDART__MEMORY_1gd228014f19cc0975ebe3e0dd2af6dd1b)
template <typename T>
struct UnifiedAllocator {
/// Allocate memory
T * allocate(std::size_t n) {
T * p = nullptr;
cudaMallocManaged(&p, n * sizeof(T));
return p;
}
/// Free memory
void deallocate(T * p, __attribute__((unused)) std::size_t n) {
cudaFree(p);
}
};
}
#endif // __UNIFIED_ALLOCATOR_HH__
c4science · Help