cms::cudacompat Namespace Reference

Classes
struct	CPUTraits
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)

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

Function Documentation

__ldg()

template<typename T >

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

inline

Definition at line 82 of file cudaCompat.h.

                               {
      return *x;
    }

Referenced by TrackingRecHit2DSOAView::__attribute__(), __attribute__(), SiPixelClustersCUDA::DeviceConstView::__attribute__(), SiPixelDigisCUDA::DeviceConstView::__attribute__(), calo::multifit::calculateChiSq(), gpuPixelDoublets::for(), pixelCPEforGPU::ParamsOnGPU::layer(), eigenSoA::ScalarSoA< uint8_t, S >::operator()(), eigenSoA::ScalarSoA< uint8_t, S >::operator[](), and calo::multifit::solve_forward_subst_matrix().

__syncthreads()

gpuVertexFinder::__syncthreads ( )

inline

Definition at line 77 of file cudaCompat.h.

{}

Referenced by gpuPixelRecHits::__attribute__(), gpuVertexFinder::__attribute__(), gpuClustering::for(), and for().

__syncthreads_and()

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

inline

Definition at line 80 of file cudaCompat.h.

{ return x; }

__syncthreads_or()

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

inline

Definition at line 79 of file cudaCompat.h.

{ return x; }

__threadfence()

void cms::cudacompat::__threadfence ( )

inline

Definition at line 78 of file cudaCompat.h.

{}

Referenced by GPUCACell::__attribute__().

atomicAdd()

template<typename T1 , typename T2 >

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

Definition at line 51 of file cudaCompat.h.

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

References a, b, and runTheMatrix::ret.

Referenced by gpuPixelRecHits::__attribute__(), cms::cuda::AtomicPairCounter::__attribute__(), cms::cuda::HistoContainer< hindex_type, S, 5 *S >::__attribute__(), cms::cuda::VecArray< T, maxSize >::emplace_back(), cms::cuda::SimpleVector< SiPixelErrorCompact >::emplace_back(), cms::cuda::SimpleVector< SiPixelErrorCompact >::extend(), gpuVertexFinder::for(), gpuClustering::for(), for(), gpuPixelDoublets::for(), if(), cms::cuda::VecArray< T, maxSize >::push_back(), cms::cuda::SimpleVector< SiPixelErrorCompact >::push_back(), and cms::cuda::SimpleVector< SiPixelErrorCompact >::shrink().

atomicCAS()

template<typename T1 , typename T2 >

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

Definition at line 36 of file cudaCompat.h.

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

References heppy_batch::val.

Referenced by GPUCACell::__attribute__().

atomicInc()

template<typename T1 , typename T2 >

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

Definition at line 43 of file cudaCompat.h.

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

References a, b, and runTheMatrix::ret.

Referenced by gpuVertexFinder::__attribute__().

atomicMax()

template<typename T1 , typename T2 >

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

Definition at line 71 of file cudaCompat.h.

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

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

Referenced by gpuPixelRecHits::__attribute__().

atomicMin()

template<typename T1 , typename T2 >

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

Definition at line 65 of file cudaCompat.h.

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

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

Referenced by gpuPixelRecHits::__attribute__(), and gpuVertexFinder::while().

atomicSub()

template<typename T1 , typename T2 >

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

Definition at line 58 of file cudaCompat.h.

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

References a, b, and runTheMatrix::ret.

Referenced by cms::cuda::HistoContainer< hindex_type, S, 5 *S >::__attribute__(), cms::cuda::VecArray< T, maxSize >::emplace_back(), cms::cuda::SimpleVector< SiPixelErrorCompact >::emplace_back(), cms::cuda::SimpleVector< SiPixelErrorCompact >::extend(), gpuPixelDoublets::for(), cms::cuda::VecArray< T, maxSize >::push_back(), cms::cuda::SimpleVector< SiPixelErrorCompact >::push_back(), and cms::cuda::SimpleVector< SiPixelErrorCompact >::shrink().

Variable Documentation

blockDim

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

Definition at line 30 of file cudaCompat.h.

Referenced by gpuPixelRecHits::__attribute__(), gpuVertexFinder::__attribute__(), gpuPixelDoublets::__attribute__(), __attribute__(), cms::cuda::HistoContainer< hindex_type, S, 5 *S >::__attribute__(), gpuCalibPixel::calibDigis(), gpuClustering::for(), and gpuVertexFinder::while().

blockIdx

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

Definition at line 32 of file cudaCompat.h.

Referenced by gpuPixelRecHits::__attribute__(), gpuPixelDoublets::__attribute__(), __attribute__(), cms::cuda::HistoContainer< hindex_type, S, 5 *S >::__attribute__(), gpuCalibPixel::calibDigis(), gpuClustering::for(), and SimPFProducer::produce().

gridDim

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

Definition at line 33 of file cudaCompat.h.

Referenced by gpuPixelDoublets::__attribute__(), __attribute__(), cms::cuda::HistoContainer< hindex_type, S, 5 *S >::__attribute__(), and gpuCalibPixel::calibDigis().

threadIdx

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

Definition at line 29 of file cudaCompat.h.

Referenced by gpuPixelRecHits::__attribute__(), gpuVertexFinder::__attribute__(), gpuPixelDoublets::__attribute__(), __attribute__(), cms::cuda::HistoContainer< hindex_type, S, 5 *S >::__attribute__(), gpuCalibPixel::calibDigis(), gpuClustering::for(), gpuVertexFinder::if(), and gpuVertexFinder::while().