FRecBufferDataGPUWrapper Struct Reference

#include <cuda_gpu_reconstruct_fourier.h>

Collaboration diagram for FRecBufferDataGPUWrapper:

Public Member Functions
	FRecBufferDataGPUWrapper (RecFourierBufferData *orig)
	~FRecBufferDataGPUWrapper ()
void	copyFrom (RecFourierBufferData *orig, int stream)
void	copyToDevice (int stream)

Public Attributes
RecFourierBufferDataGPU *	cpuCopy
RecFourierBufferDataGPU *	gpuCopy

Detailed Description

This struct simplifies work with pointers on GPU It holds a copy both in CPU and GPU memory space

Definition at line 46 of file cuda_gpu_reconstruct_fourier.h.

Constructor & Destructor Documentation

FRecBufferDataGPUWrapper()

FRecBufferDataGPUWrapper::FRecBufferDataGPUWrapper

(

RecFourierBufferData *

orig

)

Definition at line 319 of file cuda_gpu_reconstruct_fourier.cpp.

                                                                             {
    void* ptr;
    cudaMallocHost(&ptr, sizeof(RecFourierBufferDataGPU)); // allocate page-locked
    cpuCopy = (RecFourierBufferDataGPU*)ptr;
    cpuCopy->create(orig);
    gpuCopy = NULL;
}

~FRecBufferDataGPUWrapper()

FRecBufferDataGPUWrapper::~FRecBufferDataGPUWrapper

(

)

Definition at line 327 of file cuda_gpu_reconstruct_fourier.cpp.

                                                    {
    cudaFree(gpuCopy);
    gpuErrchk( cudaPeekAtLastError() );
    cpuCopy->destroy();
    cudaFreeHost(cpuCopy);
}

Member Function Documentation

copyFrom()

void FRecBufferDataGPUWrapper::copyFrom	(	RecFourierBufferData *	orig,
		int	stream
	)

Copy the content of the 'orig' buffer to new object Original buffer can be cleaned after. Works asynchronously on given stream

Definition at line 334 of file cuda_gpu_reconstruct_fourier.cpp.

                                                                              {
    cpuCopy->copyDataFrom(orig, stream);
}

copyToDevice()

void FRecBufferDataGPUWrapper::copyToDevice

(

int

stream

)

Copy CPU version to GPU, asynchronously on given stream

Definition at line 338 of file cuda_gpu_reconstruct_fourier.cpp.

                                                      {
    if (NULL == gpuCopy) {
        cudaMalloc((void **) &gpuCopy, sizeof(RecFourierBufferDataGPU));
        gpuErrchk( cudaPeekAtLastError() );
    }
    cudaMemcpyAsync(gpuCopy, cpuCopy, sizeof(RecFourierBufferDataGPU), cudaMemcpyHostToDevice, streams[stream]);
    gpuErrchk( cudaPeekAtLastError() );
}

Member Data Documentation

cpuCopy

RecFourierBufferDataGPU* FRecBufferDataGPUWrapper::cpuCopy

Definition at line 63 of file cuda_gpu_reconstruct_fourier.h.

gpuCopy

RecFourierBufferDataGPU* FRecBufferDataGPUWrapper::gpuCopy

Definition at line 66 of file cuda_gpu_reconstruct_fourier.h.

---

The documentation for this struct was generated from the following files:

• xmipp/libraries/reconstruction_cuda/cuda_gpu_reconstruct_fourier.h
• xmipp/libraries/reconstruction_cuda/cuda_gpu_reconstruct_fourier.cpp