Main Page Namespace List Class Hierarchy Alphabetical List Compound List File List Namespace Members Compound Members File Members Related Pages

msmpot_cuda_shortrng.cu File Reference

#include "msmpot_cuda.h"

Go to the source code of this file.

Defines

#define BLOCK_DIM_X   8

#define BLOCK_DIM_Y   2

#define UNROLL_Y   4

#define BLOCK_DIM_Z   8

#define REGSIZE_X   BLOCK_DIM_X

#define REGSIZE_Y   (BLOCK_DIM_Y * UNROLL_Y)

#define REGSIZE_Z   BLOCK_DIM_Z

#define REGION_SIZE   (REGSIZE_X * REGSIZE_Y * REGSIZE_Z)

#define LOG_BDIM_X   3

#define LOG_BDIM_Y   1

#define LOG_UNRL_Y   2

#define LOG_BDIM_Z   3

#define LOG_REGS_X   LOG_BDIM_X

#define LOG_REGS_Y   (LOG_BDIM_Y + LOG_UNRL_Y)

#define LOG_REGS_Z   LOG_BDIM_Z

#define LOG_REGSIZE   (LOG_REGS_X + LOG_REGS_Y + LOG_REGS_Z)

#define MASK_REGS_X   (REGSIZE_X - 1)

#define MASK_REGS_Y   (REGSIZE_Y - 1)

#define MASK_REGS_Z   (REGSIZE_Z - 1)

#define MAX_BIN_DEPTH   8

#define DSHIFT   (LOG_BDIM_X + LOG_BDIM_Y)

#define REGSXY   (REGSIZE_X * REGSIZE_Y)

#define BDIMXY   (BLOCK_DIM_X * BLOCK_DIM_Y)

#define MASK   (BDIMXY - 1)

#define DSHIFT   (LOG_BDIM_X + LOG_BDIM_Y)

#define REGSXY   (REGSIZE_X * REGSIZE_Y)

#define BDIMXY   (BLOCK_DIM_X * BLOCK_DIM_Y)

#define MASK   (BDIMXY - 1)

Functions

__global__ void cuda_shortrange_nonperiodic (float *regionBase, int zRegionDim, float dx, float dy, float dz, float rx0, float ry0, float rz0, float4 *binBase, int xBinDim, int yBinDim, int zBinDim, int bindepth, float invbx, float invby, float invbz, float cutoff2, float invcut)

__global__ void cuda_shortrange (float *regionBase, int zRegionDim, float dx, float dy, float dz, float rx0, float ry0, float rz0, float px, float py, float pz, int isperiodic, float4 *binBase, int xBinDim, int yBinDim, int zBinDim, int bindepth, float invbx, float invby, float invbz, float cutoff2, float invcut)

void Msmpot_cuda_cleanup_shortrng (MsmpotCuda *mc)

int Msmpot_cuda_setup_shortrng (MsmpotCuda *mc)

int Msmpot_cuda_compute_shortrng (MsmpotCuda *mc)

Variables

__constant__ int NbrListLen

__constant__ int3 NbrList [NBRLIST_MAXLEN]

Define Documentation

#define BDIMXY (BLOCK_DIM_X * BLOCK_DIM_Y)

#define BLOCK_DIM_X 8

Definition at line 24 of file msmpot_cuda_shortrng.cu.
Referenced by cuda_shortrange, cuda_shortrange_nonperiodic, and Msmpot_cuda_compute_shortrng.

#define BLOCK_DIM_Y 2

Definition at line 25 of file msmpot_cuda_shortrng.cu.
Referenced by cuda_shortrange, cuda_shortrange_nonperiodic, and Msmpot_cuda_compute_shortrng.

#define BLOCK_DIM_Z 8

Definition at line 27 of file msmpot_cuda_shortrng.cu.
Referenced by Msmpot_cuda_compute_shortrng.

#define DSHIFT (LOG_BDIM_X + LOG_BDIM_Y)

#define LOG_BDIM_X 3

Definition at line 35 of file msmpot_cuda_shortrng.cu.

#define LOG_BDIM_Y 1

Definition at line 36 of file msmpot_cuda_shortrng.cu.

#define LOG_BDIM_Z 3

Definition at line 38 of file msmpot_cuda_shortrng.cu.

#define LOG_REGS_X LOG_BDIM_X

Definition at line 40 of file msmpot_cuda_shortrng.cu.
Referenced by Msmpot_cuda_compute_shortrng, and Msmpot_cuda_setup_shortrng.

#define LOG_REGS_Y (LOG_BDIM_Y + LOG_UNRL_Y)

Definition at line 41 of file msmpot_cuda_shortrng.cu.
Referenced by Msmpot_cuda_compute_shortrng, and Msmpot_cuda_setup_shortrng.

#define LOG_REGS_Z LOG_BDIM_Z

Definition at line 42 of file msmpot_cuda_shortrng.cu.
Referenced by Msmpot_cuda_compute_shortrng, and Msmpot_cuda_setup_shortrng.

#define LOG_REGSIZE (LOG_REGS_X + LOG_REGS_Y + LOG_REGS_Z)

Definition at line 44 of file msmpot_cuda_shortrng.cu.

#define LOG_UNRL_Y 2

Definition at line 37 of file msmpot_cuda_shortrng.cu.

#define MASK (BDIMXY - 1)

#define MASK_REGS_X (REGSIZE_X - 1)

Definition at line 46 of file msmpot_cuda_shortrng.cu.
Referenced by Msmpot_cuda_compute_shortrng, and Msmpot_cuda_setup_shortrng.

#define MASK_REGS_Y (REGSIZE_Y - 1)

Definition at line 47 of file msmpot_cuda_shortrng.cu.
Referenced by Msmpot_cuda_compute_shortrng, and Msmpot_cuda_setup_shortrng.

#define MASK_REGS_Z (REGSIZE_Z - 1)

Definition at line 48 of file msmpot_cuda_shortrng.cu.
Referenced by Msmpot_cuda_compute_shortrng, and Msmpot_cuda_setup_shortrng.

#define MAX_BIN_DEPTH 8

Definition at line 52 of file msmpot_cuda_shortrng.cu.
Referenced by cuda_shortrange, and cuda_shortrange_nonperiodic.

#define REGION_SIZE (REGSIZE_X * REGSIZE_Y * REGSIZE_Z)

Definition at line 33 of file msmpot_cuda_shortrng.cu.
Referenced by cuda_shortrange, cuda_shortrange_nonperiodic, and Msmpot_cuda_compute_shortrng.

#define REGSIZE_X BLOCK_DIM_X

Definition at line 29 of file msmpot_cuda_shortrng.cu.
Referenced by cuda_shortrange, cuda_shortrange_nonperiodic, Msmpot_cuda_compute_shortrng, and Msmpot_cuda_setup_shortrng.

#define REGSIZE_Y (BLOCK_DIM_Y * UNROLL_Y)

Definition at line 30 of file msmpot_cuda_shortrng.cu.
Referenced by cuda_shortrange, cuda_shortrange_nonperiodic, Msmpot_cuda_compute_shortrng, and Msmpot_cuda_setup_shortrng.

#define REGSIZE_Z BLOCK_DIM_Z

Definition at line 31 of file msmpot_cuda_shortrng.cu.
Referenced by cuda_shortrange, cuda_shortrange_nonperiodic, and Msmpot_cuda_setup_shortrng.

#define REGSXY (REGSIZE_X * REGSIZE_Y)

#define UNROLL_Y 4

Definition at line 26 of file msmpot_cuda_shortrng.cu.

Function Documentation

__global__ void cuda_shortrange ( float * regionBase,

int zRegionDim,

float dx,

float dy,

float dz,

float rx0,

float ry0,

float rz0,

float px,

float py,

float pz,

int isperiodic,

float4 * binBase,

int xBinDim,

int yBinDim,

int zBinDim,

int bindepth,

float invbx,

float invby,

float invbz,

float cutoff2,

float invcut

) [static]

Definition at line 263 of file msmpot_cuda_shortrng.cu.
References bin, BLOCK_DIM_X, BLOCK_DIM_Y, IS_SET_X, IS_SET_Y, IS_SET_Z, MAX_BIN_DEPTH, n, NbrList, NbrListLen, REGION_SIZE, REGSIZE_X, REGSIZE_Y, REGSIZE_Z, and z.

__global__ void cuda_shortrange_nonperiodic ( float * regionBase,

int zRegionDim,

float dx,

float dy,

float dz,

float rx0,

float ry0,

float rz0,

float4 * binBase,

int xBinDim,

int yBinDim,

int zBinDim,

int bindepth,

float invbx,

float invby,

float invbz,

float cutoff2,

float invcut

) [static]

Definition at line 91 of file msmpot_cuda_shortrng.cu.
References bin, BLOCK_DIM_X, BLOCK_DIM_Y, MAX_BIN_DEPTH, n, NbrList, NbrListLen, REGION_SIZE, REGSIZE_X, REGSIZE_Y, REGSIZE_Z, and z.

void Msmpot_cuda_cleanup_shortrng ( MsmpotCuda * mc )

Definition at line 492 of file msmpot_cuda_shortrng.cu.
Referenced by Msmpot_cuda_cleanup.

int Msmpot_cuda_compute_shortrng ( MsmpotCuda * mc )

Definition at line 601 of file msmpot_cuda_shortrng.cu.
References Msmpot_t::a, Msmpot_t::bin, Msmpot_t::bindepth, BLOCK_DIM_X, BLOCK_DIM_Y, BLOCK_DIM_Z, CUERR, Msmpot_t::dx, Msmpot_t::dy, Msmpot_t::dz, Msmpot_t::epotmap, ERROR, Msmpot_t::invbx, Msmpot_t::invby, Msmpot_t::invbz, Msmpot_t::isperiodic, LOG_REGS_X, LOG_REGS_Y, LOG_REGS_Z, Msmpot_t::lx0, Msmpot_t::ly0, Msmpot_t::lz0, MASK_REGS_X, MASK_REGS_Y, MASK_REGS_Z, Msmpot_compute_shortrng_bin_hashing, Msmpot_compute_shortrng_linklist, MSMPOT_ERROR_CUDA_KERNEL, MSMPOT_ERROR_CUDA_MEMCPY, MSMPOT_SUCCESS, Msmpot_t::mx, Msmpot_t::my, Msmpot_t::mz, Msmpot_t::nbx, Msmpot_t::nby, Msmpot_t::nbz, Msmpot_t::nover, Msmpot_t::over, Msmpot_t::px, Msmpot_t::px0, Msmpot_t::py, Msmpot_t::py0, Msmpot_t::pz, Msmpot_t::pz0, REGION_SIZE, REGSIZE_X, REGSIZE_Y, and REPORT.
Referenced by Msmpot_compute.

int Msmpot_cuda_setup_shortrng ( MsmpotCuda * mc )

Definition at line 502 of file msmpot_cuda_shortrng.cu.
References Msmpot_t::bindepth, Msmpot_t::boff, CUERR, Msmpot_t::dx, Msmpot_t::dy, Msmpot_t::dz, ERROR, Msmpot_t::isperiodic, LOG_REGS_X, LOG_REGS_Y, LOG_REGS_Z, MASK_REGS_X, MASK_REGS_Y, MASK_REGS_Z, Msmpot_compute_shortrng_bin_neighborhood, MSMPOT_ERROR_CUDA_MALLOC, MSMPOT_ERROR_CUDA_MEMCPY, MSMPOT_ERROR_CUDA_SUPPORT, MSMPOT_ERROR_MALLOC, MSMPOT_SUCCESS, Msmpot_t::mx, Msmpot_t::my, Msmpot_t::mz, n, Msmpot_t::nboff, NbrList, NbrListLen, Msmpot_t::nbx, Msmpot_t::nby, Msmpot_t::nbz, NULL, REGSIZE_X, REGSIZE_Y, REGSIZE_Z, and REPORT.
Referenced by Msmpot_cuda_setup.

Variable Documentation

__constant__ int3 NbrList[NBRLIST_MAXLEN] [static]

Definition at line 59 of file msmpot_cuda_shortrng.cu.
Referenced by cuda_shortrange, cuda_shortrange_nonperiodic, and Msmpot_cuda_setup_shortrng.

__constant__ int NbrListLen [static]

Definition at line 58 of file msmpot_cuda_shortrng.cu.
Referenced by cuda_shortrange, cuda_shortrange_nonperiodic, and Msmpot_cuda_setup_shortrng.

Generated on Sat Apr 20 02:44:13 2024 for VMD (current) by

Defines
#define	BLOCK_DIM_X 8
#define	BLOCK_DIM_Y 2
#define	UNROLL_Y 4
#define	BLOCK_DIM_Z 8
#define	REGSIZE_X BLOCK_DIM_X
#define	REGSIZE_Y (BLOCK_DIM_Y * UNROLL_Y)
#define	REGSIZE_Z BLOCK_DIM_Z
#define	REGION_SIZE (REGSIZE_X * REGSIZE_Y * REGSIZE_Z)
#define	LOG_BDIM_X 3
#define	LOG_BDIM_Y 1
#define	LOG_UNRL_Y 2
#define	LOG_BDIM_Z 3
#define	LOG_REGS_X LOG_BDIM_X
#define	LOG_REGS_Y (LOG_BDIM_Y + LOG_UNRL_Y)
#define	LOG_REGS_Z LOG_BDIM_Z
#define	LOG_REGSIZE (LOG_REGS_X + LOG_REGS_Y + LOG_REGS_Z)
#define	MASK_REGS_X (REGSIZE_X - 1)
#define	MASK_REGS_Y (REGSIZE_Y - 1)
#define	MASK_REGS_Z (REGSIZE_Z - 1)
#define	MAX_BIN_DEPTH 8
#define	DSHIFT (LOG_BDIM_X + LOG_BDIM_Y)
#define	REGSXY (REGSIZE_X * REGSIZE_Y)
#define	BDIMXY (BLOCK_DIM_X * BLOCK_DIM_Y)
#define	MASK (BDIMXY - 1)
#define	DSHIFT (LOG_BDIM_X + LOG_BDIM_Y)
#define	REGSXY (REGSIZE_X * REGSIZE_Y)
#define	BDIMXY (BLOCK_DIM_X * BLOCK_DIM_Y)
#define	MASK (BDIMXY - 1)
Functions
__global__ void	cuda_shortrange_nonperiodic (float regionBase, int zRegionDim, float dx, float dy, float dz, float rx0, float ry0, float rz0, float4 binBase, int xBinDim, int yBinDim, int zBinDim, int bindepth, float invbx, float invby, float invbz, float cutoff2, float invcut)
__global__ void	cuda_shortrange (float regionBase, int zRegionDim, float dx, float dy, float dz, float rx0, float ry0, float rz0, float px, float py, float pz, int isperiodic, float4 binBase, int xBinDim, int yBinDim, int zBinDim, int bindepth, float invbx, float invby, float invbz, float cutoff2, float invcut)
void	Msmpot_cuda_cleanup_shortrng (MsmpotCuda *mc)
int	Msmpot_cuda_setup_shortrng (MsmpotCuda *mc)
int	Msmpot_cuda_compute_shortrng (MsmpotCuda *mc)
Variables
__constant__ int	NbrListLen
__constant__ int3	NbrList [NBRLIST_MAXLEN]