Diffusion PHPC Shallow Water Project (master) Browse

kernels.cuh
a5666521e077master

kernels.cuh
View Options

			#ifndef g
			#define g 127267.2 //Gravity, 9.82(3.6)^21000 in [km / hr^2]
			#endif
			#ifndef __KERNELS_CUH__
			#define __KERNELS_CUH__

			//----------------- Global Functions (call assignated device function)

			__global__ void copy_temp_variables_kernel(double d_H, double d_HU, double *d_HV,
			double d_Ht, double d_HUt, double *d_HVt, const int start, const int end, int nx);

			__global__ void enforce_BC_kernel(double d_Ht, double d_HUt, double *d_HVt,
			const int start, const int end, int nx);

			__global__ void FV_iterator_kernel(double d_H, double d_HU, double *d_HV,
			const double d_Zdx, const double d_Zdy, double d_Ht, double d_HUt,
			double *d_HVt, double C, double dt, const int start, const int end, int nx);

			__global__ void FV_solver_kernel(double d_H, double d_HU, double *d_HV,
			const double d_Zdx, const double d_Zdy, double d_Ht, double d_HUt,
			double *d_HVt, double C, double dt, int nx);

			__global__ void impose_tolerances_kernel(double d_Ht, double d_HUt,
			double *d_HVt, const int start, const int end, int nx);

			__global__ void find_mumax_kernel(const double H, const double HU, const double HV, int mutex,
			double* mu, const int start, const int end, int numElements);

			__global__ void find_maximum_kernel(double array, double max, int *mutex,
			const int start, const int end, unsigned int nx);

			//----------------- Device Functions

			__device__ void copy_temp_variables_device(double d_H, double d_HU, double *d_HV,
			double d_Ht, double d_HUt, double *d_HVt, const int start, const int end, int nx);

			__device__ void enforce_BC_device(double d_Ht, double d_HUt, double *d_HVt,
			const int start, const int end, int nx);

			__device__ void FV_iterator_device(double d_H, double d_HU, double *d_HV,
			const double d_Zdx, const double d_Zdy, double d_Ht, double d_HUt,
			double *d_HVt, double C, double dt, const int start, const int end, int nx);

			__device__ void impose_tolerances_device(double d_Ht, double d_HUt,
			double *d_HVt, const int start, const int end, int nx);

			__device__ void find_mumax_device(const double H, const double HU,
			const double HV, int mutex,double* mu, const int start, const int end, int nx);

			__device__ void find_maximum_device(double array, double max, int *mutex,
			const int start, const int end,unsigned int nx);

			//----------------- Additionnal Functions

			void copy_host2device(double * d_Ht,double * d_HUt,double * d_HVt,double * Ht,
			double * HUt,double * HVt,size_t memsize);

			void copy_device2host(double * H,double * HU,double * HV,double * d_H,
			double * d_HU,double * d_HV,size_t memsize);

			#endif

R6678/multi_gpu_code/kernels.cuha5666521e077master

kernels.cuhView Options

R6678/multi_gpu_code/kernels.cuh
a5666521e077master

kernels.cuh
View Options