/home/pedro/work/mdcore/src/engine_cuda.cu File Reference

#include <stdlib.h>
#include <stdio.h>
#include <pthread.h>
#include <math.h>
#include <float.h>
#include <string.h>
#include "../config.h"
#include <mpi.h>
#include <omp.h>
#include "cycle.h"
#include "errs.h"
#include "fptype.h"
#include "lock.h"
#include "part.h"
#include "cell.h"
#include "fifo.h"
#include "space.h"
#include "potential.h"
#include "runner.h"
#include "bond.h"
#include "rigid.h"
#include "angle.h"
#include "dihedral.h"
#include "exclusion.h"
#include "reader.h"
#include "engine.h"
#include "runner_cuda.h"

Defines
#define	error(id)   ( engine_err = errs_register( id , engine_err_msg[-(id)] , __LINE__ , __FUNCTION__ , __FILE__ ) )
#define	cuda_error(id)   ( engine_err = errs_register( id , cudaGetErrorString(cudaGetLastError()) , __LINE__ , __FUNCTION__ , __FILE__ ) )
Functions
__global__ void	runner_run_verlet_cuda_32 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_32 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_64 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_64 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_96 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_96 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_128 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_128 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_160 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_160 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_192 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_192 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_224 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_224 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_256 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_256 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_288 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_288 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_320 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_320 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_352 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_352 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_384 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_384 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_416 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_416 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_448 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_448 (float *forces, int *counts, int *ind)
__global__ void	runner_run_verlet_cuda_480 (float *forces, int *counts, int *ind, int verlet_rebuild)
__global__ void	runner_run_cuda_480 (float *forces, int *counts, int *ind)
int	runner_bind (cudaArray *cuArray_coeffs, cudaArray *cuArray_pind, cudaArray *cuArray_diags)
	Bind textures to the given cuda Arrays.
int	runner_parts_bind (cudaArray *cuArray_parts)
	Bind textures to the given cuda Arrays.
int	runner_parts_unbind ()
	Bind textures to the given cuda Arrays.
int	engine_cuda_setdevice (int id)
	Set the ID of the CUDA device to use.
Variables
__constant__ float4 *	cuda_parts

---

Define Documentation

#define cuda_error

(

id

)

( engine_err = errs_register( id , cudaGetErrorString(cudaGetLastError()) , __LINE__ , __FUNCTION__ , __FILE__ ) )

#define error

(

id

)

( engine_err = errs_register( id , engine_err_msg[-(id)] , __LINE__ , __FUNCTION__ , __FILE__ ) )

---

Function Documentation

int engine_cuda_setdevice

(

int

id

)

Set the ID of the CUDA device to use.

Parameters:

id	The CUDA device ID.

Returns:

engine_err_ok or < 0 on error (see engine_err).

int runner_bind	(	cudaArray *	cuArray_coeffs,
		cudaArray *	cuArray_pind,
		cudaArray *	cuArray_diags
	)

Bind textures to the given cuda Arrays.

Hack to get around the fact that textures are static and can thus not be externalized.

int runner_parts_bind

(

cudaArray *

cuArray_parts

)

Bind textures to the given cuda Arrays.

Hack to get around the fact that textures are static and can thus not be externalized.

int runner_parts_unbind

(

)

Bind textures to the given cuda Arrays.

Hack to get around the fact that textures are static and can thus not be externalized.

__global__ void runner_run_cuda_128	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_160	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_192	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_224	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_256	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_288	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_32	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_320	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_352	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_384	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_416	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_448	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_480	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_64	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_cuda_96	(	float *	forces,
		int *	counts,
		int *	ind
	)

__global__ void runner_run_verlet_cuda_128	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_160	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_192	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_224	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_256	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_288	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_32	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_320	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_352	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_384	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_416	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_448	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_480	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_64	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

__global__ void runner_run_verlet_cuda_96	(	float *	forces,
		int *	counts,
		int *	ind,
		int	verlet_rebuild
	)

---

Variable Documentation

__constant__ float4* cuda_parts