Homec4science
Diffusion tamaas-public (master) Browse

tamaas-public/src/gpu/unified_allocator.hh
4ecfb2213b97master

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 <cuda_runtime_api.h>
#include <memory>
/* -------------------------------------------------------------------------- */
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); }
};
} // namespace tamaas
#endif // __UNIFIED_ALLOCATOR_HH__
c4science · Help