CMS 3D CMS Logo

Classes | Functions | Variables
pixelgpudetails Namespace Reference

Classes

struct  DetIdGPU
 
class  Packing
 
struct  Pixel
 
class  PixelRecHitGPUKernel
 
class  SiPixelRawToClusterGPUKernel
 

Functions

__host__ __device__ uint32_t pack (uint32_t row, uint32_t col, uint32_t adc)
 
__host__ constexpr __device__ Packing packing ()
 
constexpr uint32_t pixelToChannel (int row, int col)
 

Variables

const uint32_t ADC_bits = 8
 
const uint32_t ADC_mask = ~(~uint32_t(0) << ADC_bits)
 
const uint32_t ADC_shift = 0
 
const uint32_t bladeMask = 0x3F
 
const uint32_t bladeStartBit = 12
 
const uint32_t COL_bits_l1 = 6
 
const uint32_t COL_mask = ~(~uint32_t(0) << COL_bits_l1)
 
const uint32_t COL_shift = ROW_shift + ROW_bits_l1
 
const uint32_t DCOL_bits = 5
 
const uint32_t DCOL_mask = ~(~uint32_t(0) << DCOL_bits)
 
const uint32_t DCOL_shift = PXID_shift + PXID_bits
 
const uint32_t diskMask = 0xF
 
const uint32_t diskStartBit = 18
 
const uint32_t ERROR_mask = ~(~uint32_t(0) << ROC_bits_l1)
 
const uint32_t ladderMask = 0xFF
 
const uint32_t ladderStartBit = 12
 
const uint32_t layerMask = 0xF
 
const uint32_t layerStartBit = 20
 
const uint32_t LINK_bits = 6
 
const uint32_t LINK_bits_l1 = 6
 
const uint32_t LINK_mask = ~(~uint32_t(0) << LINK_bits_l1)
 
const uint32_t LINK_shift = ROC_shift + ROC_bits_l1
 
constexpr unsigned int MAX_FED = 150
 
constexpr unsigned int MAX_LINK = 48
 
constexpr unsigned int MAX_ROC = 8
 
constexpr unsigned int MAX_SIZE = MAX_FED * MAX_LINK * MAX_ROC
 
constexpr unsigned int MAX_SIZE_BYTE_BOOL = MAX_SIZE * sizeof(unsigned char)
 
const uint32_t MAX_WORD = 2000
 
const uint32_t maxROCIndex = 8
 
const uint32_t moduleMask = 0x3FF
 
const uint32_t moduleStartBit = 2
 
const uint32_t numColsInRoc = 52
 
const uint32_t numRowsInRoc = 80
 
const uint32_t OMIT_ERR_bits = 1
 
const uint32_t OMIT_ERR_mask = ~(~uint32_t(0) << OMIT_ERR_bits)
 
const uint32_t OMIT_ERR_shift = 20
 
const uint32_t panelMask = 0x3
 
const uint32_t panelStartBit = 10
 
const uint32_t PXID_bits = 8
 
const uint32_t PXID_mask = ~(~uint32_t(0) << PXID_bits)
 
const uint32_t PXID_shift = ADC_shift + ADC_bits
 
const uint32_t ROC_bits = 5
 
const uint32_t ROC_bits_l1 = 5
 
const uint32_t ROC_mask = ~(~uint32_t(0) << ROC_bits_l1)
 
const uint32_t ROC_shift = DCOL_shift + DCOL_bits
 
const uint32_t ROW_bits_l1 = 7
 
const uint32_t ROW_mask = ~(~uint32_t(0) << ROW_bits_l1)
 
const uint32_t ROW_shift = ADC_shift + ADC_bits
 

Function Documentation

◆ pack()

__host__ __device__ uint32_t pixelgpudetails::pack ( uint32_t  row,
uint32_t  col,
uint32_t  adc 
)
inline

Definition at line 138 of file SiPixelRawToClusterGPUKernel.h.

138  {
139  constexpr Packing thePacking = packing();
140  adc = std::min(adc, thePacking.max_adc);
141 
142  return (row << thePacking.row_shift) | (col << thePacking.column_shift) | (adc << thePacking.adc_shift);
143  }

References gpuClustering::adc, cuy::col, min(), and packing().

◆ packing()

__host__ constexpr __device__ Packing pixelgpudetails::packing ( )
inlineconstexpr

Definition at line 136 of file SiPixelRawToClusterGPUKernel.h.

136 { return Packing(11, 11, 0, 10); }

Referenced by pack(), and pixelToChannel().

◆ pixelToChannel()

constexpr uint32_t pixelgpudetails::pixelToChannel ( int  row,
int  col 
)
constexpr

Definition at line 145 of file SiPixelRawToClusterGPUKernel.h.

145  {
146  constexpr Packing thePacking = packing();
147  return (row << thePacking.column_width) | col;
148  }

References cuy::col, and packing().

Referenced by Pixel3DDigitizerAlgorithm::induce_signal().

Variable Documentation

◆ ADC_bits

const uint32_t pixelgpudetails::ADC_bits = 8

◆ ADC_mask

const uint32_t pixelgpudetails::ADC_mask = ~(~uint32_t(0) << ADC_bits)

Definition at line 76 of file SiPixelRawToClusterGPUKernel.h.

◆ ADC_shift

const uint32_t pixelgpudetails::ADC_shift = 0

Definition at line 60 of file SiPixelRawToClusterGPUKernel.h.

◆ bladeMask

const uint32_t pixelgpudetails::bladeMask = 0x3F

Definition at line 39 of file SiPixelRawToClusterGPUKernel.h.

◆ bladeStartBit

const uint32_t pixelgpudetails::bladeStartBit = 12

Definition at line 32 of file SiPixelRawToClusterGPUKernel.h.

◆ COL_bits_l1

const uint32_t pixelgpudetails::COL_bits_l1 = 6

Definition at line 50 of file SiPixelRawToClusterGPUKernel.h.

◆ COL_mask

const uint32_t pixelgpudetails::COL_mask = ~(~uint32_t(0) << COL_bits_l1)

Definition at line 72 of file SiPixelRawToClusterGPUKernel.h.

◆ COL_shift

const uint32_t pixelgpudetails::COL_shift = ROW_shift + ROW_bits_l1

Definition at line 67 of file SiPixelRawToClusterGPUKernel.h.

◆ DCOL_bits

const uint32_t pixelgpudetails::DCOL_bits = 5

◆ DCOL_mask

const uint32_t pixelgpudetails::DCOL_mask = ~(~uint32_t(0) << DCOL_bits)

Definition at line 74 of file SiPixelRawToClusterGPUKernel.h.

◆ DCOL_shift

const uint32_t pixelgpudetails::DCOL_shift = PXID_shift + PXID_bits

Definition at line 62 of file SiPixelRawToClusterGPUKernel.h.

◆ diskMask

const uint32_t pixelgpudetails::diskMask = 0xF

Definition at line 38 of file SiPixelRawToClusterGPUKernel.h.

◆ diskStartBit

const uint32_t pixelgpudetails::diskStartBit = 18

Definition at line 31 of file SiPixelRawToClusterGPUKernel.h.

◆ ERROR_mask

const uint32_t pixelgpudetails::ERROR_mask = ~(~uint32_t(0) << ROC_bits_l1)

◆ ladderMask

const uint32_t pixelgpudetails::ladderMask = 0xFF

Definition at line 35 of file SiPixelRawToClusterGPUKernel.h.

◆ ladderStartBit

const uint32_t pixelgpudetails::ladderStartBit = 12

Definition at line 27 of file SiPixelRawToClusterGPUKernel.h.

◆ layerMask

const uint32_t pixelgpudetails::layerMask = 0xF

Definition at line 34 of file SiPixelRawToClusterGPUKernel.h.

◆ layerStartBit

const uint32_t pixelgpudetails::layerStartBit = 20

Definition at line 26 of file SiPixelRawToClusterGPUKernel.h.

◆ LINK_bits

const uint32_t pixelgpudetails::LINK_bits = 6

◆ LINK_bits_l1

const uint32_t pixelgpudetails::LINK_bits_l1 = 6

Definition at line 48 of file SiPixelRawToClusterGPUKernel.h.

◆ LINK_mask

const uint32_t pixelgpudetails::LINK_mask = ~(~uint32_t(0) << LINK_bits_l1)

◆ LINK_shift

const uint32_t pixelgpudetails::LINK_shift = ROC_shift + ROC_bits_l1

◆ MAX_FED

constexpr unsigned int pixelgpudetails::MAX_FED = 150
constexpr

Definition at line 7 of file SiPixelROCsStatusAndMapping.h.

◆ MAX_LINK

constexpr unsigned int pixelgpudetails::MAX_LINK = 48
constexpr

◆ MAX_ROC

constexpr unsigned int pixelgpudetails::MAX_ROC = 8
constexpr

◆ MAX_SIZE

constexpr unsigned int pixelgpudetails::MAX_SIZE = MAX_FED * MAX_LINK * MAX_ROC
constexpr

◆ MAX_SIZE_BYTE_BOOL

constexpr unsigned int pixelgpudetails::MAX_SIZE_BYTE_BOOL = MAX_SIZE * sizeof(unsigned char)
constexpr

◆ MAX_WORD

const uint32_t pixelgpudetails::MAX_WORD = 2000

Definition at line 58 of file SiPixelRawToClusterGPUKernel.h.

◆ maxROCIndex

const uint32_t pixelgpudetails::maxROCIndex = 8

Definition at line 54 of file SiPixelRawToClusterGPUKernel.h.

◆ moduleMask

const uint32_t pixelgpudetails::moduleMask = 0x3FF

Definition at line 36 of file SiPixelRawToClusterGPUKernel.h.

◆ moduleStartBit

const uint32_t pixelgpudetails::moduleStartBit = 2

Definition at line 28 of file SiPixelRawToClusterGPUKernel.h.

◆ numColsInRoc

const uint32_t pixelgpudetails::numColsInRoc = 52

Definition at line 56 of file SiPixelRawToClusterGPUKernel.h.

◆ numRowsInRoc

const uint32_t pixelgpudetails::numRowsInRoc = 80

Definition at line 55 of file SiPixelRawToClusterGPUKernel.h.

◆ OMIT_ERR_bits

const uint32_t pixelgpudetails::OMIT_ERR_bits = 1

Definition at line 52 of file SiPixelRawToClusterGPUKernel.h.

◆ OMIT_ERR_mask

const uint32_t pixelgpudetails::OMIT_ERR_mask = ~(~uint32_t(0) << OMIT_ERR_bits)

◆ OMIT_ERR_shift

const uint32_t pixelgpudetails::OMIT_ERR_shift = 20

◆ panelMask

const uint32_t pixelgpudetails::panelMask = 0x3

Definition at line 37 of file SiPixelRawToClusterGPUKernel.h.

◆ panelStartBit

const uint32_t pixelgpudetails::panelStartBit = 10

Definition at line 30 of file SiPixelRawToClusterGPUKernel.h.

◆ PXID_bits

const uint32_t pixelgpudetails::PXID_bits = 8

◆ PXID_mask

const uint32_t pixelgpudetails::PXID_mask = ~(~uint32_t(0) << PXID_bits)

Definition at line 75 of file SiPixelRawToClusterGPUKernel.h.

◆ PXID_shift

const uint32_t pixelgpudetails::PXID_shift = ADC_shift + ADC_bits

Definition at line 61 of file SiPixelRawToClusterGPUKernel.h.

◆ ROC_bits

const uint32_t pixelgpudetails::ROC_bits = 5

◆ ROC_bits_l1

const uint32_t pixelgpudetails::ROC_bits_l1 = 5

Definition at line 49 of file SiPixelRawToClusterGPUKernel.h.

◆ ROC_mask

const uint32_t pixelgpudetails::ROC_mask = ~(~uint32_t(0) << ROC_bits_l1)

◆ ROC_shift

const uint32_t pixelgpudetails::ROC_shift = DCOL_shift + DCOL_bits

◆ ROW_bits_l1

const uint32_t pixelgpudetails::ROW_bits_l1 = 7

Definition at line 51 of file SiPixelRawToClusterGPUKernel.h.

◆ ROW_mask

const uint32_t pixelgpudetails::ROW_mask = ~(~uint32_t(0) << ROW_bits_l1)

Definition at line 73 of file SiPixelRawToClusterGPUKernel.h.

◆ ROW_shift

const uint32_t pixelgpudetails::ROW_shift = ADC_shift + ADC_bits

Definition at line 66 of file SiPixelRawToClusterGPUKernel.h.

pixelgpudetails::packing
__host__ constexpr __device__ Packing packing()
Definition: SiPixelRawToClusterGPUKernel.h:136
min
T min(T a, T b)
Definition: MathUtil.h:58
gpuClustering::adc
uint16_t *__restrict__ uint16_t const *__restrict__ adc
Definition: gpuClusterChargeCut.h:20
cuy.col
col
Definition: cuy.py:1010