TrackingRecHit2DSOAView Class Reference

#include <TrackingRecHit2DSOAView.h>

Public Types
using	AverageGeometry = pixelTopology::AverageGeometry
using	hindex_type = uint32_t
using	PhiBinner = cms::cuda::HistoContainer< int16_t, 256, -1, 8 *sizeof(int16_t), hindex_type, pixelTopology::maxLayers >
using	Status = SiPixelHitStatus

Public Member Functions
__device__	__attribute__ ((always_inline)) uint32_t nHits() const
__device__	__attribute__ ((always_inline)) uint32_t nMaxModules() const
__device__	__attribute__ ((always_inline)) float &xLocal(int i)
__device__	__attribute__ ((always_inline)) float xLocal(int i) const
__device__	__attribute__ ((always_inline)) float &yLocal(int i)
__device__	__attribute__ ((always_inline)) float yLocal(int i) const
__device__	__attribute__ ((always_inline)) float &xerrLocal(int i)
__device__	__attribute__ ((always_inline)) float xerrLocal(int i) const
__device__	__attribute__ ((always_inline)) float &yerrLocal(int i)
__device__	__attribute__ ((always_inline)) float yerrLocal(int i) const
__device__	__attribute__ ((always_inline)) float &xGlobal(int i)
__device__	__attribute__ ((always_inline)) float xGlobal(int i) const
__device__	__attribute__ ((always_inline)) float &yGlobal(int i)
__device__	__attribute__ ((always_inline)) float yGlobal(int i) const
__device__	__attribute__ ((always_inline)) float &zGlobal(int i)
__device__	__attribute__ ((always_inline)) float zGlobal(int i) const
__device__	__attribute__ ((always_inline)) float &rGlobal(int i)
__device__	__attribute__ ((always_inline)) float rGlobal(int i) const
__device__	__attribute__ ((always_inline)) int16_t &iphi(int i)
__device__	__attribute__ ((always_inline)) int16_t iphi(int i) const
__device__	__attribute__ ((always_inline)) void setChargeAndStatus(int i
__device__	__attribute__ ((always_inline)) uint32_t charge(int i) const
__device__	__attribute__ ((always_inline)) Status status(int i) const
__device__	__attribute__ ((always_inline)) int16_t &clusterSizeX(int i)
__device__	__attribute__ ((always_inline)) int16_t clusterSizeX(int i) const
__device__	__attribute__ ((always_inline)) int16_t &clusterSizeY(int i)
__device__	__attribute__ ((always_inline)) int16_t clusterSizeY(int i) const
__device__	__attribute__ ((always_inline)) uint16_t &detectorIndex(int i)
__device__	__attribute__ ((always_inline)) uint16_t detectorIndex(int i) const
__device__	__attribute__ ((always_inline)) pixelCPEforGPU
__device__	__attribute__ ((always_inline)) uint32_t const *hitsLayerStart() const
__device__	__attribute__ ((always_inline)) PhiBinner &phiBinner()
__device__	__attribute__ ((always_inline)) PhiBinner const &phiBinner() const
__device__	__attribute__ ((always_inline)) AverageGeometry &averageGeometry()
__device__	__attribute__ ((always_inline)) AverageGeometry const &averageGeometry() const

Public Attributes
__device__ uint32_t	ich
	ich = (w << 24)
__device__ uint32_t Status	is
	m_chargeAndStatus [i] = ich
uint32_t	w = *reinterpret_cast<uint8_t*>(&is)

Static Private Member Functions
static constexpr uint32_t	chargeMask ()

Private Attributes
AverageGeometry *	m_averageGeometry
uint32_t *	m_chargeAndStatus
pixelCPEforGPU::ParamsOnGPU const *	m_cpeParams
uint16_t *	m_detInd
uint32_t *	m_hitsLayerStart
uint32_t const *	m_hitsModuleStart
int16_t *	m_iphi
uint32_t	m_nHits
uint32_t	m_nMaxModules
PhiBinner *	m_phiBinner
PhiBinner::index_type *	m_phiBinnerStorage
float *	m_rg
float *	m_xerr
float *	m_xg
float *	m_xl
int16_t *	m_xsize
float *	m_yerr
float *	m_yg
float *	m_yl
int16_t *	m_ysize
float *	m_zg

Friends
template<typename >
class	TrackingRecHit2DHeterogeneous
class	TrackingRecHit2DReduced

Detailed Description

Definition at line 16 of file TrackingRecHit2DSOAView.h.

Member Typedef Documentation

AverageGeometry

using TrackingRecHit2DSOAView::AverageGeometry = pixelTopology::AverageGeometry

Definition at line 26 of file TrackingRecHit2DSOAView.h.

hindex_type

using TrackingRecHit2DSOAView::hindex_type = uint32_t

Definition at line 21 of file TrackingRecHit2DSOAView.h.

PhiBinner

using TrackingRecHit2DSOAView::PhiBinner = cms::cuda:: HistoContainer<int16_t, 256, -1, 8 * sizeof(int16_t), hindex_type, pixelTopology::maxLayers>

Definition at line 24 of file TrackingRecHit2DSOAView.h.

Status

using TrackingRecHit2DSOAView::Status = SiPixelHitStatus

Definition at line 18 of file TrackingRecHit2DSOAView.h.

Member Function Documentation

__attribute__() [1/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 32 of file TrackingRecHit2DSOAView.h.

References m_nHits.

{ return m_nHits; }

__attribute__() [2/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 33 of file TrackingRecHit2DSOAView.h.

References m_nMaxModules.

{ return m_nMaxModules; }

__attribute__() [3/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 35 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_xl.

{ return m_xl[i]; }

__attribute__() [4/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 36 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_xl.

{ return __ldg(m_xl + i); }

__attribute__() [5/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 37 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_yl.

{ return m_yl[i]; }

__attribute__() [6/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 38 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_yl.

{ return __ldg(m_yl + i); }

__attribute__() [7/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 40 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_xerr.

{ return m_xerr[i]; }

__attribute__() [8/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 41 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_xerr.

{ return __ldg(m_xerr + i); }

__attribute__() [9/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 42 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_yerr.

{ return m_yerr[i]; }

__attribute__() [10/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 43 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_yerr.

{ return __ldg(m_yerr + i); }

__attribute__() [11/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 45 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_xg.

{ return m_xg[i]; }

__attribute__() [12/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 46 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_xg.

{ return __ldg(m_xg + i); }

__attribute__() [13/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 47 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_yg.

{ return m_yg[i]; }

__attribute__() [14/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 48 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_yg.

{ return __ldg(m_yg + i); }

__attribute__() [15/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 49 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_zg.

{ return m_zg[i]; }

__attribute__() [16/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 50 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_zg.

{ return __ldg(m_zg + i); }

__attribute__() [17/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 51 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_rg.

{ return m_rg[i]; }

__attribute__() [18/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 52 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_rg.

{ return __ldg(m_rg + i); }

__attribute__() [19/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 54 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_iphi.

{ return m_iphi[i]; }

__attribute__() [20/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 55 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_iphi.

{ return __ldg(m_iphi + i); }

__attribute__() [21/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  )

inline

__attribute__() [22/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 64 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_chargeAndStatus.

{ return __ldg(m_chargeAndStatus + i) & 0xFFFFFF; }

__attribute__() [23/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 66 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, m_chargeAndStatus, and w.

                                                        {
    uint8_t w = __ldg(m_chargeAndStatus + i) >> 24;
    return *reinterpret_cast<Status*>(&w);
  }

__attribute__() [24/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 71 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_xsize.

{ return m_xsize[i]; }

__attribute__() [25/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 72 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_xsize.

{ return __ldg(m_xsize + i); }

__attribute__() [26/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 73 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_ysize.

{ return m_ysize[i]; }

__attribute__() [27/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 74 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_ysize.

{ return __ldg(m_ysize + i); }

__attribute__() [28/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 75 of file TrackingRecHit2DSOAView.h.

References mps_fire::i, and m_detInd.

{ return m_detInd[i]; }

__attribute__() [29/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 76 of file TrackingRecHit2DSOAView.h.

References cms::cudacompat::__ldg(), mps_fire::i, and m_detInd.

{ return __ldg(m_detInd + i); }

__attribute__() [30/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  )

inline

Definition at line 78 of file TrackingRecHit2DSOAView.h.

References m_cpeParams.

                                                                                { return *m_cpeParams; }

  __device__ __forceinline__ uint32_t hitsModuleStart(int i) const { return __ldg(m_hitsModuleStart + i); }

  __device__ __forceinline__ uint32_t* hitsLayerStart() { return m_hitsLayerStart; }

__attribute__() [31/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const

inline

Definition at line 83 of file TrackingRecHit2DSOAView.h.

References m_hitsLayerStart.

{ return m_hitsLayerStart; }

__attribute__() [32/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 85 of file TrackingRecHit2DSOAView.h.

References m_phiBinner.

{ return *m_phiBinner; }

__attribute__() [33/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const &

inline

Definition at line 86 of file TrackingRecHit2DSOAView.h.

References m_phiBinner.

{ return *m_phiBinner; }

__attribute__() [34/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) &

inline

Definition at line 88 of file TrackingRecHit2DSOAView.h.

References m_averageGeometry.

{ return *m_averageGeometry; }

__attribute__() [35/35]

__device__ TrackingRecHit2DSOAView::__attribute__ ( (always_inline)  ) const &

inline

Definition at line 89 of file TrackingRecHit2DSOAView.h.

References m_averageGeometry.

{ return *m_averageGeometry; }

chargeMask()

static constexpr uint32_t TrackingRecHit2DSOAView::chargeMask ( )

inlinestaticprivate

Definition at line 101 of file TrackingRecHit2DSOAView.h.

{ return (1 << 24) - 1; }

Friends And Related Function Documentation

TrackingRecHit2DHeterogeneous

template<typename >

friend class TrackingRecHit2DHeterogeneous

friend

Definition at line 29 of file TrackingRecHit2DSOAView.h.

TrackingRecHit2DReduced

friend class TrackingRecHit2DReduced

friend

Definition at line 30 of file TrackingRecHit2DSOAView.h.

Member Data Documentation

ich [1/2]

__device__ uint32_t TrackingRecHit2DSOAView::ich

Definition at line 57 of file TrackingRecHit2DSOAView.h.

ich [2/2]

TrackingRecHit2DSOAView::ich = (w << 24)

Definition at line 60 of file TrackingRecHit2DSOAView.h.

is

__device__ uint32_t Status TrackingRecHit2DSOAView::is

Initial value:

{
    ich = std::min(ich, chargeMask())

Definition at line 57 of file TrackingRecHit2DSOAView.h.

m_averageGeometry

AverageGeometry* TrackingRecHit2DSOAView::m_averageGeometry

private

Definition at line 109 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_chargeAndStatus [1/2]

TrackingRecHit2DSOAView::m_chargeAndStatus[i] = ich

Definition at line 61 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous(), and TrackingRecHit2DReduced::TrackingRecHit2DReduced().

m_chargeAndStatus [2/2]

uint32_t* TrackingRecHit2DSOAView::m_chargeAndStatus

private

Definition at line 102 of file TrackingRecHit2DSOAView.h.

m_cpeParams

pixelCPEforGPU::ParamsOnGPU const* TrackingRecHit2DSOAView::m_cpeParams

private

Definition at line 110 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_detInd

uint16_t* TrackingRecHit2DSOAView::m_detInd

private

Definition at line 105 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous(), and TrackingRecHit2DReduced::TrackingRecHit2DReduced().

m_hitsLayerStart

uint32_t* TrackingRecHit2DSOAView::m_hitsLayerStart

private

Definition at line 113 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_hitsModuleStart

uint32_t const* TrackingRecHit2DSOAView::m_hitsModuleStart

private

Definition at line 111 of file TrackingRecHit2DSOAView.h.

Referenced by TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_iphi

int16_t* TrackingRecHit2DSOAView::m_iphi

private

Definition at line 98 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_nHits

uint32_t TrackingRecHit2DSOAView::m_nHits

private

Definition at line 118 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_nMaxModules

uint32_t TrackingRecHit2DSOAView::m_nMaxModules

private

Definition at line 119 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_phiBinner

PhiBinner* TrackingRecHit2DSOAView::m_phiBinner

private

Definition at line 115 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_phiBinnerStorage

PhiBinner::index_type* TrackingRecHit2DSOAView::m_phiBinnerStorage

private

Definition at line 116 of file TrackingRecHit2DSOAView.h.

Referenced by TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_rg

float * TrackingRecHit2DSOAView::m_rg

private

Definition at line 97 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_xerr

float* TrackingRecHit2DSOAView::m_xerr

private

Definition at line 94 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous(), and TrackingRecHit2DReduced::TrackingRecHit2DReduced().

m_xg

float* TrackingRecHit2DSOAView::m_xg

private

Definition at line 97 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_xl

float* TrackingRecHit2DSOAView::m_xl

private

Definition at line 93 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous(), and TrackingRecHit2DReduced::TrackingRecHit2DReduced().

m_xsize

int16_t* TrackingRecHit2DSOAView::m_xsize

private

Definition at line 103 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_yerr

float * TrackingRecHit2DSOAView::m_yerr

private

Definition at line 94 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous(), and TrackingRecHit2DReduced::TrackingRecHit2DReduced().

m_yg

float * TrackingRecHit2DSOAView::m_yg

private

Definition at line 97 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_yl

float * TrackingRecHit2DSOAView::m_yl

private

Definition at line 93 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous(), and TrackingRecHit2DReduced::TrackingRecHit2DReduced().

m_ysize

int16_t* TrackingRecHit2DSOAView::m_ysize

private

Definition at line 104 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

m_zg

float * TrackingRecHit2DSOAView::m_zg

private

Definition at line 97 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

w

uint32_t TrackingRecHit2DSOAView::w = *reinterpret_cast<uint8_t*>(&is)

Definition at line 59 of file TrackingRecHit2DSOAView.h.

Referenced by __attribute__().