mdcore  0.1.5
Defines | Functions | Variables
/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:
idThe 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.

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
 All Data Structures Files Functions Variables Typedefs Enumerator Defines