#include <config/config.hpp>
#include "magnetostatics/dipolar_direct_sum_gpu_cuda.cuh"
#include "cuda/utils.cuh"
#include <thrust/device_ptr.h>
#include <thrust/reduce.h>
#include <cuda.h>

Functions
__device__ float	scalar_product (float const a, float const b)

__device__ void	vector_product (float const a, float const b, float *out)

__device__ void	get_mi_vector_dds (float res[3], float const a[3], float const b[3], float const box_l[3], int const periodic[3])

__device__ void	dipole_ia_force (float const pf, float const dr[3], float const const dip1, float const const dip2, float const f1, float const torque1, float const torque2, float const dip_fld1, float *const dip_fld2)

__device__ float	dipole_ia_energy (float pf, float const r1, float const r2, float const dip1, float const dip2, float box_l[3], int periodic[3])

__global__ void	DipolarDirectSum_kernel_force (float const pf, unsigned int n, float const const pos, float const const dip, float dip_fld, float const f, float *const torque, float const box_l[3], int const periodic[3], int const n_replicas)

__device__ void	dds_sumReduction (float input, float sum)

__global__ void	DipolarDirectSum_kernel_energy (float pf, unsigned int n, float const const pos, float const const dip, float box_l[3], int periodic[3], float *energySum)

void	copy_box_data (float box_l_gpu, int periodic_gpu, float const box_l, int const periodic)

void	DipolarDirectSum_kernel_wrapper_force (float k, unsigned int n, float const const pos, float const const dip, float dip_fld, float f, float *torque, float box_l[3], int periodic[3], int n_replicas)

void	DipolarDirectSum_kernel_wrapper_energy (float k, unsigned int n, float const const pos, float const const dip, float box_l[3], int periodic[3], float *E)

Function Documentation

◆ copy_box_data()

void copy_box_data	(	float **	box_l_gpu,
		int **	periodic_gpu,
		float const *	box_l,
		int const *	periodic
	)

inline

Definition at line 336 of file dipolar_direct_sum_gpu_cuda.cu.

References cuda_safe_mem, and stream.

Referenced by DipolarDirectSum_kernel_wrapper_energy(), and DipolarDirectSum_kernel_wrapper_force().

◆ dds_sumReduction()

__device__ void dds_sumReduction	(	float *	input,
		float *	sum
	)

Definition at line 288 of file dipolar_direct_sum_gpu_cuda.cu.

References stream.

Referenced by DipolarDirectSum_kernel_energy().

◆ DipolarDirectSum_kernel_energy()

__global__ void DipolarDirectSum_kernel_energy	(	float	pf,
		unsigned int	n,
		float const *const	pos,
		float const *const	dip,
		float	box_l[3],
		int	periodic[3],
		float *	energySum
	)

Definition at line 304 of file dipolar_direct_sum_gpu_cuda.cu.

References dds_sumReduction(), dipole_ia_energy(), and stream.

Referenced by DipolarDirectSum_kernel_wrapper_energy().

◆ DipolarDirectSum_kernel_force()

__global__ void DipolarDirectSum_kernel_force	(	float const	pf,
		unsigned int	n,
		float const *const	pos,
		float const *const	dip,
		float *	dip_fld,
		float *const	f,
		float *const	torque,
		float const	box_l[3],
		int const	periodic[3],
		int const	n_replicas
	)

Definition at line 156 of file dipolar_direct_sum_gpu_cuda.cu.

References dipole_ia_force(), get_mi_vector_dds(), and stream.

Referenced by DipolarDirectSum_kernel_wrapper_force().

◆ DipolarDirectSum_kernel_wrapper_energy()

void DipolarDirectSum_kernel_wrapper_energy	(	float	k,
		unsigned int	n,
		float const *const	pos,
		float const *const	dip,
		float	box_l[3],
		int	periodic[3],
		float *	E
	)

Definition at line 379 of file dipolar_direct_sum_gpu_cuda.cu.

References block(), copy_box_data(), cuda_safe_mem, DipolarDirectSum_kernel_energy(), KERNELCALL_shared, and stream.

Referenced by DipolarDirectSumGpu::long_range_energy().

◆ DipolarDirectSum_kernel_wrapper_force()

void DipolarDirectSum_kernel_wrapper_force	(	float	k,
		unsigned int	n,
		float const *const	pos,
		float const *const	dip,
		float *	dip_fld,
		float *	f,
		float *	torque,
		float	box_l[3],
		int	periodic[3],
		int	n_replicas
	)

Definition at line 347 of file dipolar_direct_sum_gpu_cuda.cu.

References block(), copy_box_data(), DipolarDirectSum_kernel_force(), KERNELCALL, and stream.

Referenced by DipolarDirectSumGpu::add_long_range_forces().

◆ dipole_ia_energy()

__device__ float dipole_ia_energy	(	float	pf,
		float const *	r1,
		float const *	r2,
		float const *	dip1,
		float const *	dip2,
		float	box_l[3],
		int	periodic[3]
	)

Definition at line 130 of file dipolar_direct_sum_gpu_cuda.cu.

References get_mi_vector_dds(), scalar_product(), and stream.

Referenced by DipolarDirectSum_kernel_energy().

◆ dipole_ia_force()

__device__ void dipole_ia_force	(	float const	pf,
		float const	dr[3],
		float const *const	dip1,
		float const *const	dip2,
		float *const	f1,
		float *const	torque1,
		float *const	torque2,
		float *const	dip_fld1,
		float *const	dip_fld2
	)