cms::cudacompat Namespace Reference

Classes
struct	CPUTraits
struct	dim3
struct	GPUTraits
struct	HostTraits

Functions
template<typename T >
T	__ldg (T const *x)
void	__syncthreads ()
bool	__syncthreads_and (bool x)
bool	__syncthreads_or (bool x)
void	__threadfence ()
template<typename T1 , typename T2 >
T1	atomicAdd (T1 *a, T2 b)
template<typename T1 , typename T2 >
T1	atomicCAS (T1 *address, T1 compare, T2 val)
template<typename T1 , typename T2 >
T1	atomicInc (T1 *a, T2 b)
template<typename T1 , typename T2 >
T1	atomicMax (T1 *a, T2 b)
template<typename T1 , typename T2 >
T1	atomicMin (T1 *a, T2 b)
template<typename T1 , typename T2 >
T1	atomicSub (T1 *a, T2 b)
void	resetGrid ()

Variables
const dim3	blockDim = {1, 1, 1}
thread_local dim3	blockIdx
thread_local dim3	gridDim
const dim3	threadIdx = {0, 0, 0}

Function Documentation

__ldg()

template<typename T >

T cms::cudacompat::__ldg ( T const *  x )

inline

Definition at line 77 of file cudaCompat.h.

                               {
      return *x;
    }

Referenced by calo::multifit::calculateChiSq(), eigenSoA::ScalarSoA< T, S >::operator()(), eigenSoA::ScalarSoA< T, S >::operator[](), and calo::multifit::solve_forward_subst_matrix().

__syncthreads()

void cms::cudacompat::__syncthreads ( )

inline

Definition at line 72 of file cudaCompat.h.

{}

__syncthreads_and()

bool cms::cudacompat::__syncthreads_and ( bool  x )

inline

Definition at line 75 of file cudaCompat.h.

{ return x; }

__syncthreads_or()

bool cms::cudacompat::__syncthreads_or ( bool  x )

inline

Definition at line 74 of file cudaCompat.h.

{ return x; }

__threadfence()

void cms::cudacompat::__threadfence ( )

inline

Definition at line 73 of file cudaCompat.h.

{}

atomicAdd()

template<typename T1 , typename T2 >

T1 cms::cudacompat::atomicAdd	(	T1 *	a,
		T2	b
	)

Definition at line 46 of file cudaCompat.h.

                              {
      auto ret = *a;
      (*a) += b;
      return ret;
    }

References a, b, and runTheMatrix::ret.

Referenced by cms::cuda::AtomicPairCounter::__attribute__(), cms::cuda::HistoContainer< T, NBINS, SIZE, S, I, NHISTS >::__attribute__(), cms::cuda::VecArray< T, maxSize >::emplace_back(), cms::cuda::SimpleVector< T >::emplace_back(), cms::cuda::SimpleVector< T >::extend(), cms::cuda::VecArray< T, maxSize >::push_back(), cms::cuda::SimpleVector< T >::push_back(), and cms::cuda::SimpleVector< T >::shrink().

atomicCAS()

template<typename T1 , typename T2 >

T1 cms::cudacompat::atomicCAS	(	T1 *	address,
		T1	compare,
		T2	val
	)

Definition at line 31 of file cudaCompat.h.

                                                  {
      T1 old = *address;
      *address = old == compare ? val : old;
      return old;
    }

References heppy_batch::val.

atomicInc()

template<typename T1 , typename T2 >

T1 cms::cudacompat::atomicInc	(	T1 *	a,
		T2	b
	)

Definition at line 38 of file cudaCompat.h.

                              {
      auto ret = *a;
      if ((*a) < T1(b))
        (*a)++;
      return ret;
    }

References a, b, and runTheMatrix::ret.

atomicMax()

template<typename T1 , typename T2 >

T1 cms::cudacompat::atomicMax	(	T1 *	a,
		T2	b
	)

Definition at line 66 of file cudaCompat.h.

                              {
      auto ret = *a;
      *a = std::max(*a, T1(b));
      return ret;
    }

References a, b, SiStripPI::max, and runTheMatrix::ret.

atomicMin()

template<typename T1 , typename T2 >

T1 cms::cudacompat::atomicMin	(	T1 *	a,
		T2	b
	)

Definition at line 60 of file cudaCompat.h.

                              {
      auto ret = *a;
      *a = std::min(*a, T1(b));
      return ret;
    }

References a, b, min(), and runTheMatrix::ret.

atomicSub()

template<typename T1 , typename T2 >

T1 cms::cudacompat::atomicSub	(	T1 *	a,
		T2	b
	)

Definition at line 53 of file cudaCompat.h.

                              {
      auto ret = *a;
      (*a) -= b;
      return ret;
    }

References a, b, and runTheMatrix::ret.

Referenced by cms::cuda::HistoContainer< T, NBINS, SIZE, S, I, NHISTS >::__attribute__(), cms::cuda::VecArray< T, maxSize >::emplace_back(), cms::cuda::SimpleVector< T >::emplace_back(), cms::cuda::SimpleVector< T >::extend(), cms::cuda::VecArray< T, maxSize >::push_back(), cms::cuda::SimpleVector< T >::push_back(), and cms::cuda::SimpleVector< T >::shrink().

resetGrid()

void cms::cudacompat::resetGrid ( )

inline

Definition at line 81 of file cudaCompat.h.

                            {
      blockIdx = {0, 0, 0};
      gridDim = {1, 1, 1};
    }

References blockIdx, and gridDim.

Variable Documentation

blockDim

const dim3 cms::cudacompat::blockDim = {1, 1, 1}

Definition at line 25 of file cudaCompat.h.

Referenced by cms::cuda::HistoContainer< T, NBINS, SIZE, S, I, NHISTS >::__attribute__().

blockIdx

thread_local dim3 cms::cudacompat::blockIdx

Definition at line 5 of file cudaCompat.cc.

Referenced by cms::cuda::HistoContainer< T, NBINS, SIZE, S, I, NHISTS >::__attribute__(), SimPFProducer::produce(), and resetGrid().

gridDim

thread_local dim3 cms::cudacompat::gridDim

Definition at line 6 of file cudaCompat.cc.

Referenced by cms::cuda::HistoContainer< T, NBINS, SIZE, S, I, NHISTS >::__attribute__(), and resetGrid().

threadIdx

const dim3 cms::cudacompat::threadIdx = {0, 0, 0}

Definition at line 24 of file cudaCompat.h.

Referenced by cms::cuda::HistoContainer< T, NBINS, SIZE, S, I, NHISTS >::__attribute__().