Page Menu
Home
c4science
Search
Configure Global Search
Log In
Files
F67217760
fftransform_cufft.cpp
No One
Temporary
Actions
Download File
Edit File
Delete File
View Transforms
Subscribe
Mute Notifications
Award Token
Subscribers
None
File Metadata
Details
File Info
Storage
Attached
Created
Thu, Jun 20, 22:03
Size
3 KB
Mime Type
text/x-c++
Expires
Sat, Jun 22, 22:03 (1 d, 23 h)
Engine
blob
Format
Raw Data
Handle
18331691
Attached To
rTAMAAS tamaas
fftransform_cufft.cpp
View Options
/**
* @file
*
* @author Lucas Frérot <lucas.frerot@epfl.ch>
*
* @section LICENSE
*
* Copyright (©) 2016 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/>.
*
*/
/* -------------------------------------------------------------------------- */
#include "fftransform_cufft.hh"
#define MAX_THREADS 1024
__BEGIN_TAMAAS__
template <typename T, UInt dim>
FFTransformCUFFT<T, dim>::FFTransformCUFFT(Grid<T, dim>& real,
GridHermitian<T, dim>& spectral)
: FFTransform<T, dim>(real, spectral) {
const UInt size = real.sizes()[0];
const int components = real.getNbComponents();
// fftw parameters
int rank = dim; // dimension of fft
int n[dim] = {0};
std::copy(real.sizes().begin(), real.sizes().end(),
n); // size of individual fft
int howmany = components; // how many fft to compute
int idist = 1, odist = 1; // components are next to each other in memory
int istride = components, ostride = components;
int *inembed = nullptr, *onembed = nullptr; // row major
cufftResult forward_res =
cufftPlanMany(&forward_plan, rank, n, inembed, istride, idist, onembed,
ostride, odist, CUFFT_D2Z, howmany);
cufftResult backward_res =
cufftPlanMany(&backward_plan, rank, n, onembed, ostride, odist, inembed,
istride, idist, CUFFT_Z2D, howmany);
if (forward_res != CUFFT_SUCCESS)
TAMAAS_EXCEPTION("Forward cufft plan creation failed");
if (backward_res != CUFFT_SUCCESS)
TAMAAS_EXCEPTION("Backward cufft plan creation failed");
}
/* -------------------------------------------------------------------------- */
template <typename T, UInt dim>
FFTransformCUFFT<T, dim>::~FFTransformCUFFT() {
cufftDestroy(forward_plan);
cufftDestroy(backward_plan);
}
/* -------------------------------------------------------------------------- */
template <typename T, UInt dim>
void FFTransformCUFFT<T, dim>::forwardTransform() {
cufftDoubleComplex* out =
reinterpret_cast<cufftDoubleComplex*>(this->spectral.getInternalData());
if (cufftExecD2Z(forward_plan, this->real.getInternalData(), out) !=
CUFFT_SUCCESS)
TAMAAS_EXCEPTION("Forward transform fail");
cudaDeviceSynchronize(); ///< TODO ask the SCITAS guys
}
/* -------------------------------------------------------------------------- */
template <typename T, UInt dim>
void FFTransformCUFFT<T, dim>::backwardTransform() {
cufftDoubleComplex* out =
reinterpret_cast<cufftDoubleComplex*>(this->spectral.getInternalData());
if (cufftExecZ2D(backward_plan, out, this->real.getInternalData()) !=
CUFFT_SUCCESS)
TAMAAS_EXCEPTION("Backward transform fail");
cudaDeviceSynchronize(); ///< TODO ask the SCITAS guys
this->normalize();
}
/* -------------------------------------------------------------------------- */
template class FFTransformCUFFT<Real, 1>;
template class FFTransformCUFFT<Real, 2>;
template class FFTransformCUFFT<Real, 3>;
__END_TAMAAS__
Event Timeline
Log In to Comment