TrackingRecHit2DHeterogeneous< Traits > Class Template Reference

#include <TrackingRecHit2DHeterogeneous.h>

Public Types
using	PhiBinner = TrackingRecHit2DSOAView::PhiBinner
enum	Storage16 { Storage16::kDetId = 0, Storage16::kPhi = 1, Storage16::kXSize = 2, Storage16::kYSize = 3 }
enum	Storage32 {   Storage32::kXLocal = 0, Storage32::kYLocal = 1, Storage32::kXerror = 2, Storage32::kYerror = 3,   Storage32::kCharge = 4, Storage32::kXGlobal = 5, Storage32::kYGlobal = 6, Storage32::kZGlobal = 7,   Storage32::kRGlobal = 8, Storage32::kPhiStorage = 9, Storage32::kLayers = 10 }
template<typename T >
using	unique_ptr = typename Traits::template unique_ptr< T >

Public Member Functions
void	copyFromGPU (TrackingRecHit2DHeterogeneous< cms::cudacompat::GPUTraits > const *input, cudaStream_t stream)
auto	hitsLayerStart ()
auto	hitsModuleStart () const
cms::cuda::host::unique_ptr< uint32_t[]>	hitsModuleStartToHostAsync (cudaStream_t stream) const
auto	iphi ()
cms::cuda::host::unique_ptr< float[]>	localCoordToHostAsync (cudaStream_t stream) const
auto	nHits () const
auto	nMaxModules () const
auto	offsetBPIX2 () const
TrackingRecHit2DHeterogeneous &	operator= (const TrackingRecHit2DHeterogeneous &)=delete
TrackingRecHit2DHeterogeneous &	operator= (TrackingRecHit2DHeterogeneous &&)=default
auto	phiBinner ()
auto	phiBinnerStorage ()
cms::cuda::host::unique_ptr< uint16_t[]>	store16ToHostAsync (cudaStream_t stream) const
cms::cuda::host::unique_ptr< float[]>	store32ToHostAsync (cudaStream_t stream) const
	TrackingRecHit2DHeterogeneous ()=default
	TrackingRecHit2DHeterogeneous (uint32_t nHits, bool isPhase2, int32_t offsetBPIX2, pixelCPEforGPU::ParamsOnGPU const *cpeParams, uint32_t const *hitsModuleStart, cudaStream_t stream, TrackingRecHit2DHeterogeneous< cms::cudacompat::GPUTraits > const *input=nullptr)
	TrackingRecHit2DHeterogeneous (float *store32, uint16_t *store16, uint32_t *modules, int nHits, cudaStream_t stream=nullptr)
	TrackingRecHit2DHeterogeneous (const TrackingRecHit2DHeterogeneous &)=delete
	TrackingRecHit2DHeterogeneous (TrackingRecHit2DHeterogeneous &&)=default
TrackingRecHit2DSOAView *	view ()
TrackingRecHit2DSOAView const *	view () const
	~TrackingRecHit2DHeterogeneous ()=default

Private Attributes
unique_ptr< TrackingRecHit2DSOAView::AverageGeometry >	m_AverageGeometryStore
uint32_t *	m_hitsLayerStart
uint32_t const *	m_hitsModuleStart
int16_t *	m_iphi
uint32_t	m_nHits
uint32_t	m_nMaxModules
int32_t	m_offsetBPIX2
PhiBinner *	m_phiBinner
PhiBinner::index_type *	m_phiBinnerStorage
unique_ptr< TrackingRecHit2DSOAView::PhiBinner >	m_PhiBinnerStore
unique_ptr< uint16_t[]>	m_store16
unique_ptr< float[]>	m_store32
unique_ptr< TrackingRecHit2DSOAView >	m_view

Static Private Attributes
static constexpr uint32_t	n16 = 4
static constexpr uint32_t	n32 = 10

Detailed Description

template<typename Traits>
class TrackingRecHit2DHeterogeneous< Traits >

Definition at line 9 of file TrackingRecHit2DHeterogeneous.h.

Member Typedef Documentation

PhiBinner

template<typename Traits>

using TrackingRecHit2DHeterogeneous< Traits >::PhiBinner = TrackingRecHit2DSOAView::PhiBinner

Definition at line 35 of file TrackingRecHit2DHeterogeneous.h.

unique_ptr

template<typename Traits>

template<typename T >

using TrackingRecHit2DHeterogeneous< Traits >::unique_ptr = typename Traits::template unique_ptr<T>

Definition at line 33 of file TrackingRecHit2DHeterogeneous.h.

Member Enumeration Documentation

Storage16

template<typename Traits>

enum TrackingRecHit2DHeterogeneous::Storage16

strong

Enumerator
kDetId
kPhi
kXSize
kYSize

Definition at line 25 of file TrackingRecHit2DHeterogeneous.h.

                       {
    kDetId = 0,
    kPhi = 1,
    kXSize = 2,
    kYSize = 3,
  };

Storage32

template<typename Traits>

enum TrackingRecHit2DHeterogeneous::Storage32

strong

Enumerator
kXLocal
kYLocal
kXerror
kYerror
kCharge
kXGlobal
kYGlobal
kZGlobal
kRGlobal
kPhiStorage
kLayers

Definition at line 11 of file TrackingRecHit2DHeterogeneous.h.

                       {
    kXLocal = 0,
    kYLocal = 1,
    kXerror = 2,
    kYerror = 3,
    kCharge = 4,
    kXGlobal = 5,
    kYGlobal = 6,
    kZGlobal = 7,
    kRGlobal = 8,
    kPhiStorage = 9,
    kLayers = 10
  };

Constructor & Destructor Documentation

TrackingRecHit2DHeterogeneous() [1/5]

template<typename Traits>

TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous ( )

default

TrackingRecHit2DHeterogeneous() [2/5]

template<typename Traits >

TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous ( uint32_t  nHits, bool  isPhase2, int32_t  offsetBPIX2, pixelCPEforGPU::ParamsOnGPU const *  cpeParams, uint32_t const *  hitsModuleStart, cudaStream_t  stream, TrackingRecHit2DHeterogeneous< cms::cudacompat::GPUTraits > const *  input = nullptr  )

explicit

Definition at line 114 of file TrackingRecHit2DHeterogeneous.h.

References cms::cuda::assert(), cms::cuda::copyAsync(), TrackingRecHit2DHeterogeneous< Traits >::copyFromGPU(), TrackingRecHit2DHeterogeneous< Traits >::hitsModuleStart(), mps_fire::i, input, HLT_2022v12_cff::isPhase2, TrackingRecHit2DHeterogeneous< Traits >::kCharge, TrackingRecHit2DHeterogeneous< Traits >::kDetId, TrackingRecHit2DHeterogeneous< Traits >::kLayers, TrackingRecHit2DHeterogeneous< Traits >::kPhi, TrackingRecHit2DHeterogeneous< Traits >::kPhiStorage, TrackingRecHit2DHeterogeneous< Traits >::kRGlobal, TrackingRecHit2DHeterogeneous< Traits >::kXerror, TrackingRecHit2DHeterogeneous< Traits >::kXGlobal, TrackingRecHit2DHeterogeneous< Traits >::kXLocal, TrackingRecHit2DHeterogeneous< Traits >::kXSize, TrackingRecHit2DHeterogeneous< Traits >::kYerror, TrackingRecHit2DHeterogeneous< Traits >::kYGlobal, TrackingRecHit2DHeterogeneous< Traits >::kYLocal, TrackingRecHit2DHeterogeneous< Traits >::kYSize, TrackingRecHit2DHeterogeneous< Traits >::kZGlobal, TrackingRecHit2DSOAView::m_averageGeometry, TrackingRecHit2DHeterogeneous< Traits >::m_AverageGeometryStore, TrackingRecHit2DSOAView::m_chargeAndStatus, TrackingRecHit2DSOAView::m_cpeParams, TrackingRecHit2DSOAView::m_detInd, TrackingRecHit2DHeterogeneous< Traits >::m_hitsLayerStart, TrackingRecHit2DSOAView::m_hitsLayerStart, TrackingRecHit2DSOAView::m_hitsModuleStart, TrackingRecHit2DSOAView::m_iphi, TrackingRecHit2DHeterogeneous< Traits >::m_iphi, TrackingRecHit2DSOAView::m_nHits, TrackingRecHit2DHeterogeneous< Traits >::m_nMaxModules, TrackingRecHit2DSOAView::m_nMaxModules, TrackingRecHit2DHeterogeneous< Traits >::m_phiBinner, TrackingRecHit2DSOAView::m_phiBinner, TrackingRecHit2DHeterogeneous< Traits >::m_phiBinnerStorage, TrackingRecHit2DSOAView::m_phiBinnerStorage, TrackingRecHit2DHeterogeneous< Traits >::m_PhiBinnerStore, TrackingRecHit2DSOAView::m_rg, TrackingRecHit2DHeterogeneous< Traits >::m_store16, TrackingRecHit2DHeterogeneous< Traits >::m_store32, TrackingRecHit2DHeterogeneous< Traits >::m_view, TrackingRecHit2DSOAView::m_xerr, TrackingRecHit2DSOAView::m_xg, TrackingRecHit2DSOAView::m_xl, TrackingRecHit2DSOAView::m_xsize, TrackingRecHit2DSOAView::m_yerr, TrackingRecHit2DSOAView::m_yg, TrackingRecHit2DSOAView::m_yl, TrackingRecHit2DSOAView::m_ysize, TrackingRecHit2DSOAView::m_zg, TrackingRecHit2DHeterogeneous< Traits >::n16, TrackingRecHit2DHeterogeneous< Traits >::n32, TrackingRecHit2DHeterogeneous< Traits >::nHits(), phase1PixelTopology::numberOfLayers, phase2PixelTopology::numberOfLayers, phase1PixelTopology::numberOfModules, phase2PixelTopology::numberOfModules, cms::cuda::stream, svgfig::template(), and TrackingRecHit2DHeterogeneous< Traits >::view().

    : m_nHits(nHits), m_offsetBPIX2(offsetBPIX2), m_hitsModuleStart(hitsModuleStart) {
  auto view = Traits::template make_host_unique<TrackingRecHit2DSOAView>(stream);

  m_nMaxModules = isPhase2 ? phase2PixelTopology::numberOfModules : phase1PixelTopology::numberOfModules;

  view->m_nHits = nHits;
  view->m_nMaxModules = m_nMaxModules;
  m_view = Traits::template make_unique<TrackingRecHit2DSOAView>(stream);  // leave it on host and pass it by value?
  m_AverageGeometryStore = Traits::template make_unique<TrackingRecHit2DSOAView::AverageGeometry>(stream);
  view->m_averageGeometry = m_AverageGeometryStore.get();
  view->m_cpeParams = cpeParams;
  view->m_hitsModuleStart = hitsModuleStart;

  // if empy do not bother
  if (0 == nHits) {
    if constexpr (std::is_same_v<Traits, cms::cudacompat::GPUTraits>) {
      cms::cuda::copyAsync(m_view, view, stream);
    } else {
      m_view.reset(view.release());  // NOLINT: std::move() breaks CUDA version
    }
    return;
  }

  // the single arrays are not 128 bit alligned...
  // the hits are actually accessed in order only in building
  // if ordering is relevant they may have to be stored phi-ordered by layer or so
  // this will break 1to1 correspondence with cluster and module locality
  // so unless proven VERY inefficient we keep it ordered as generated

  // host copy is "reduced"  (to be reviewed at some point)
  if constexpr (std::is_same_v<Traits, cms::cudacompat::HostTraits>) {
    // it has to compile for ALL cases
    copyFromGPU(input, stream);
  } else {
    assert(input == nullptr);

    auto nL = isPhase2 ? phase2PixelTopology::numberOfLayers : phase1PixelTopology::numberOfLayers;

    m_store16 = Traits::template make_unique<uint16_t[]>(nHits * n16, stream);
    m_store32 = Traits::template make_unique<float[]>(nHits * n32 + nL + 1, stream);
    m_PhiBinnerStore = Traits::template make_unique<TrackingRecHit2DSOAView::PhiBinner>(stream);
  }

  static_assert(sizeof(TrackingRecHit2DSOAView::hindex_type) == sizeof(float));
  static_assert(sizeof(TrackingRecHit2DSOAView::hindex_type) == sizeof(TrackingRecHit2DSOAView::PhiBinner::index_type));

  auto get32 = [&](Storage32 i) { return m_store32.get() + static_cast<int>(i) * nHits; };

  // copy all the pointers
  m_phiBinner = view->m_phiBinner = m_PhiBinnerStore.get();
  m_phiBinnerStorage = view->m_phiBinnerStorage =
      reinterpret_cast<TrackingRecHit2DSOAView::PhiBinner::index_type*>(get32(Storage32::kPhiStorage));

  view->m_xl = get32(Storage32::kXLocal);
  view->m_yl = get32(Storage32::kYLocal);
  view->m_xerr = get32(Storage32::kXerror);
  view->m_yerr = get32(Storage32::kYerror);
  view->m_chargeAndStatus = reinterpret_cast<uint32_t*>(get32(Storage32::kCharge));

  if constexpr (!std::is_same_v<Traits, cms::cudacompat::HostTraits>) {
    assert(input == nullptr);
    view->m_xg = get32(Storage32::kXGlobal);
    view->m_yg = get32(Storage32::kYGlobal);
    view->m_zg = get32(Storage32::kZGlobal);
    view->m_rg = get32(Storage32::kRGlobal);

    auto get16 = [&](Storage16 i) { return m_store16.get() + static_cast<int>(i) * nHits; };
    m_iphi = view->m_iphi = reinterpret_cast<int16_t*>(get16(Storage16::kPhi));

    view->m_xsize = reinterpret_cast<int16_t*>(get16(Storage16::kXSize));
    view->m_ysize = reinterpret_cast<int16_t*>(get16(Storage16::kYSize));
    view->m_detInd = get16(Storage16::kDetId);

    m_phiBinner = view->m_phiBinner = m_PhiBinnerStore.get();
    m_hitsLayerStart = view->m_hitsLayerStart = reinterpret_cast<uint32_t*>(get32(Storage32::kLayers));
  }

  // transfer view
  if constexpr (std::is_same_v<Traits, cms::cudacompat::GPUTraits>) {
    cms::cuda::copyAsync(m_view, view, stream);
  } else {
    m_view.reset(view.release());  // NOLINT: std::move() breaks CUDA version
  }
}

TrackingRecHit2DHeterogeneous() [3/5]

template<typename Traits >

TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous ( float *  store32, uint16_t *  store16, uint32_t *  modules, int  nHits, cudaStream_t  stream = nullptr  )

explicit

Definition at line 209 of file TrackingRecHit2DHeterogeneous.h.

References filterCSVwithJSON::copy, cms::cuda::copyAsync(), mps_fire::i, TrackingRecHit2DHeterogeneous< Traits >::kCharge, TrackingRecHit2DHeterogeneous< Traits >::kDetId, TrackingRecHit2DHeterogeneous< Traits >::kPhi, TrackingRecHit2DHeterogeneous< Traits >::kPhiStorage, TrackingRecHit2DHeterogeneous< Traits >::kRGlobal, TrackingRecHit2DHeterogeneous< Traits >::kXerror, TrackingRecHit2DHeterogeneous< Traits >::kXGlobal, TrackingRecHit2DHeterogeneous< Traits >::kXLocal, TrackingRecHit2DHeterogeneous< Traits >::kXSize, TrackingRecHit2DHeterogeneous< Traits >::kYerror, TrackingRecHit2DHeterogeneous< Traits >::kYGlobal, TrackingRecHit2DHeterogeneous< Traits >::kYLocal, TrackingRecHit2DHeterogeneous< Traits >::kYSize, TrackingRecHit2DHeterogeneous< Traits >::kZGlobal, TrackingRecHit2DSOAView::m_averageGeometry, TrackingRecHit2DHeterogeneous< Traits >::m_AverageGeometryStore, TrackingRecHit2DSOAView::m_chargeAndStatus, TrackingRecHit2DSOAView::m_detInd, TrackingRecHit2DHeterogeneous< Traits >::m_hitsModuleStart, TrackingRecHit2DSOAView::m_hitsModuleStart, TrackingRecHit2DSOAView::m_iphi, TrackingRecHit2DHeterogeneous< Traits >::m_iphi, TrackingRecHit2DSOAView::m_nHits, TrackingRecHit2DHeterogeneous< Traits >::m_phiBinner, TrackingRecHit2DSOAView::m_phiBinner, TrackingRecHit2DHeterogeneous< Traits >::m_phiBinnerStorage, TrackingRecHit2DSOAView::m_phiBinnerStorage, TrackingRecHit2DHeterogeneous< Traits >::m_PhiBinnerStore, TrackingRecHit2DSOAView::m_rg, TrackingRecHit2DHeterogeneous< Traits >::m_store16, TrackingRecHit2DHeterogeneous< Traits >::m_store32, TrackingRecHit2DHeterogeneous< Traits >::m_view, TrackingRecHit2DSOAView::m_xerr, TrackingRecHit2DSOAView::m_xg, TrackingRecHit2DSOAView::m_xl, TrackingRecHit2DSOAView::m_xsize, TrackingRecHit2DSOAView::m_yerr, TrackingRecHit2DSOAView::m_yg, TrackingRecHit2DSOAView::m_yl, TrackingRecHit2DSOAView::m_ysize, TrackingRecHit2DSOAView::m_zg, eostools::move(), TrackingRecHit2DHeterogeneous< Traits >::n16, TrackingRecHit2DHeterogeneous< Traits >::n32, TrackingRecHit2DHeterogeneous< Traits >::nHits(), cms::cuda::stream, svgfig::template(), and TrackingRecHit2DHeterogeneous< Traits >::view().

    : m_nHits(nHits), m_hitsModuleStart(modules) {
  auto view = Traits::template make_host_unique<TrackingRecHit2DSOAView>(stream);

  m_view = Traits::template make_unique<TrackingRecHit2DSOAView>(stream);

  view->m_nHits = nHits;

  if (0 == nHits) {
    if constexpr (std::is_same_v<Traits, cms::cudacompat::GPUTraits>) {
      cms::cuda::copyAsync(m_view, view, stream);
    } else {
      m_view = std::move(view);
    }
    return;
  }

  m_store16 = Traits::template make_unique<uint16_t[]>(nHits * n16, stream);
  m_store32 = Traits::template make_unique<float[]>(nHits * n32, stream);
  m_PhiBinnerStore = Traits::template make_unique<TrackingRecHit2DSOAView::PhiBinner>(stream);
  m_AverageGeometryStore = Traits::template make_unique<TrackingRecHit2DSOAView::AverageGeometry>(stream);

  view->m_averageGeometry = m_AverageGeometryStore.get();
  view->m_hitsModuleStart = m_hitsModuleStart;

  //store transfer
  if constexpr (std::is_same_v<Traits, cms::cudacompat::GPUTraits>) {
    cms::cuda::copyAsync(m_store16, store16, stream);
    cms::cuda::copyAsync(m_store32, store32, stream);
  } else {
    std::copy(store32, store32 + nHits * n32, m_store32.get());  // want to copy it
    std::copy(store16, store16 + nHits * n16, m_store16.get());
  }

  //getters
  auto get32 = [&](Storage32 i) { return m_store32.get() + static_cast<int>(i) * nHits; };
  auto get16 = [&](Storage16 i) { return m_store16.get() + static_cast<int>(i) * nHits; };

  //Store 32
  view->m_xl = get32(Storage32::kXLocal);
  view->m_yl = get32(Storage32::kYLocal);
  view->m_xerr = get32(Storage32::kXerror);
  view->m_yerr = get32(Storage32::kYerror);
  view->m_chargeAndStatus = reinterpret_cast<uint32_t*>(get32(Storage32::kCharge));
  view->m_xg = get32(Storage32::kXGlobal);
  view->m_yg = get32(Storage32::kYGlobal);
  view->m_zg = get32(Storage32::kZGlobal);
  view->m_rg = get32(Storage32::kRGlobal);

  m_phiBinner = view->m_phiBinner = m_PhiBinnerStore.get();
  m_phiBinnerStorage = view->m_phiBinnerStorage =
      reinterpret_cast<TrackingRecHit2DSOAView::PhiBinner::index_type*>(get32(Storage32::kPhiStorage));

  //Store 16
  view->m_detInd = get16(Storage16::kDetId);
  m_iphi = view->m_iphi = reinterpret_cast<int16_t*>(get16(Storage16::kPhi));
  view->m_xsize = reinterpret_cast<int16_t*>(get16(Storage16::kXSize));
  view->m_ysize = reinterpret_cast<int16_t*>(get16(Storage16::kYSize));

  // transfer view
  if constexpr (std::is_same_v<Traits, cms::cudacompat::GPUTraits>) {
    cms::cuda::copyAsync(m_view, view, stream);
  } else {
    m_view = std::move(view);
  }
}

~TrackingRecHit2DHeterogeneous()

template<typename Traits>

TrackingRecHit2DHeterogeneous< Traits >::~TrackingRecHit2DHeterogeneous ( )

default

TrackingRecHit2DHeterogeneous() [4/5]

template<typename Traits>

TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous ( const TrackingRecHit2DHeterogeneous< Traits > &  )

delete

TrackingRecHit2DHeterogeneous() [5/5]

template<typename Traits>

TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous ( TrackingRecHit2DHeterogeneous< Traits > &&  )

default

Member Function Documentation

copyFromGPU()

template<typename Traits>

void TrackingRecHit2DHeterogeneous< Traits >::copyFromGPU	(	TrackingRecHit2DHeterogeneous< cms::cudacompat::GPUTraits > const *	input,
		cudaStream_t	stream
	)

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

hitsLayerStart()

template<typename Traits>

auto TrackingRecHit2DHeterogeneous< Traits >::hitsLayerStart ( )

inline

Definition at line 65 of file TrackingRecHit2DHeterogeneous.h.

References TrackingRecHit2DHeterogeneous< Traits >::m_hitsLayerStart.

{ return m_hitsLayerStart; }

hitsModuleStart()

template<typename Traits>

auto TrackingRecHit2DHeterogeneous< Traits >::hitsModuleStart ( ) const

inline

Definition at line 64 of file TrackingRecHit2DHeterogeneous.h.

References TrackingRecHit2DHeterogeneous< Traits >::m_hitsModuleStart.

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

{ return m_hitsModuleStart; }

hitsModuleStartToHostAsync()

cms::cuda::host::unique_ptr< uint32_t[]> TrackingRecHit2DGPU::hitsModuleStartToHostAsync

(

cudaStream_t

stream

)

const

Definition at line 29 of file TrackingRecHit2DHeterogeneous.cc.

References cudaCheck, TrackingRecHit2DHeterogeneous< Traits >::m_hitsModuleStart, TrackingRecHit2DHeterogeneous< Traits >::nMaxModules(), runTheMatrix::ret, and cms::cuda::stream.

                                                                                                           {
  auto ret = cms::cuda::make_host_unique<uint32_t[]>(nMaxModules() + 1, stream);
  cudaCheck(
      cudaMemcpyAsync(ret.get(), m_hitsModuleStart, sizeof(uint32_t) * (nMaxModules() + 1), cudaMemcpyDefault, stream));
  return ret;
}

iphi()

template<typename Traits>

auto TrackingRecHit2DHeterogeneous< Traits >::iphi ( )

inline

Definition at line 68 of file TrackingRecHit2DHeterogeneous.h.

References TrackingRecHit2DHeterogeneous< Traits >::m_iphi.

{ return m_iphi; }

localCoordToHostAsync()

cms::cuda::host::unique_ptr< float[]> TrackingRecHit2DGPU::localCoordToHostAsync

(

cudaStream_t

stream

)

const

Definition at line 8 of file TrackingRecHit2DHeterogeneous.cc.

References cms::cuda::copyAsync(), TrackingRecHit2DHeterogeneous< Traits >::m_store32, TrackingRecHit2DHeterogeneous< Traits >::nHits(), runTheMatrix::ret, and cms::cuda::stream.

                                                                                                   {
  auto ret = cms::cuda::make_host_unique<float[]>(5 * nHits(), stream);
  cms::cuda::copyAsync(ret, m_store32, 5 * nHits(), stream);
  return ret;
}

nHits()

template<typename Traits>

auto TrackingRecHit2DHeterogeneous< Traits >::nHits ( ) const

inline

Definition at line 60 of file TrackingRecHit2DHeterogeneous.h.

References TrackingRecHit2DHeterogeneous< Traits >::m_nHits.

Referenced by TrackingRecHit2DHeterogeneous< Traits >::localCoordToHostAsync(), CAHitNtupletGeneratorOnGPU::makeTuples(), CAHitNtupletGeneratorOnGPU::makeTuplesAsync(), TrackingRecHit2DHeterogeneous< Traits >::store16ToHostAsync(), TrackingRecHit2DHeterogeneous< Traits >::store32ToHostAsync(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

{ return m_nHits; }

nMaxModules()

template<typename Traits>

auto TrackingRecHit2DHeterogeneous< Traits >::nMaxModules ( ) const

inline

Definition at line 61 of file TrackingRecHit2DHeterogeneous.h.

References TrackingRecHit2DHeterogeneous< Traits >::m_nMaxModules.

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

{ return m_nMaxModules; }

offsetBPIX2()

template<typename Traits>

auto TrackingRecHit2DHeterogeneous< Traits >::offsetBPIX2 ( ) const

inline

Definition at line 62 of file TrackingRecHit2DHeterogeneous.h.

References TrackingRecHit2DHeterogeneous< Traits >::m_offsetBPIX2.

{ return m_offsetBPIX2; }

operator=() [1/2]

template<typename Traits>

TrackingRecHit2DHeterogeneous& TrackingRecHit2DHeterogeneous< Traits >::operator= ( const TrackingRecHit2DHeterogeneous< Traits > &  )

delete

operator=() [2/2]

template<typename Traits>

TrackingRecHit2DHeterogeneous& TrackingRecHit2DHeterogeneous< Traits >::operator= ( TrackingRecHit2DHeterogeneous< Traits > &&  )

default

phiBinner()

template<typename Traits>

auto TrackingRecHit2DHeterogeneous< Traits >::phiBinner ( )

inline

Definition at line 66 of file TrackingRecHit2DHeterogeneous.h.

References TrackingRecHit2DHeterogeneous< Traits >::m_phiBinner.

{ return m_phiBinner; }

phiBinnerStorage()

template<typename Traits>

auto TrackingRecHit2DHeterogeneous< Traits >::phiBinnerStorage ( )

inline

Definition at line 67 of file TrackingRecHit2DHeterogeneous.h.

References TrackingRecHit2DHeterogeneous< Traits >::m_phiBinnerStorage.

{ return m_phiBinnerStorage; }

store16ToHostAsync()

cms::cuda::host::unique_ptr< uint16_t[]> TrackingRecHit2DGPU::store16ToHostAsync

(

cudaStream_t

stream

)

const

Definition at line 22 of file TrackingRecHit2DHeterogeneous.cc.

References cms::cuda::copyAsync(), TrackingRecHit2DHeterogeneous< Traits >::m_store16, TrackingRecHit2DHeterogeneous< Traits >::n16, TrackingRecHit2DHeterogeneous< Traits >::nHits(), runTheMatrix::ret, and cms::cuda::stream.

                                                                                                   {
  auto ret = cms::cuda::make_host_unique<uint16_t[]>(static_cast<int>(n16) * nHits(), stream);
  cms::cuda::copyAsync(ret, m_store16, static_cast<int>(n16) * nHits(), stream);
  return ret;
}

store32ToHostAsync()

cms::cuda::host::unique_ptr< float[]> TrackingRecHit2DGPU::store32ToHostAsync

(

cudaStream_t

stream

)

const

Definition at line 15 of file TrackingRecHit2DHeterogeneous.cc.

References cms::cuda::copyAsync(), TrackingRecHit2DHeterogeneous< Traits >::m_store32, TrackingRecHit2DHeterogeneous< Traits >::n32, TrackingRecHit2DHeterogeneous< Traits >::nHits(), runTheMatrix::ret, and cms::cuda::stream.

                                                                                                {
  auto ret = cms::cuda::make_host_unique<float[]>(static_cast<int>(n32) * nHits(), stream);
  cms::cuda::copyAsync(ret, m_store32, static_cast<int>(n32) * nHits(), stream);
  return ret;
}

view() [1/2]

template<typename Traits>

TrackingRecHit2DSOAView* TrackingRecHit2DHeterogeneous< Traits >::view ( )

inline

Definition at line 57 of file TrackingRecHit2DHeterogeneous.h.

References TrackingRecHit2DHeterogeneous< Traits >::m_view.

Referenced by CAHitNtupletGeneratorOnGPU::makeTuples(), CAHitNtupletGeneratorOnGPU::makeTuplesAsync(), and TrackingRecHit2DHeterogeneous< Traits >::TrackingRecHit2DHeterogeneous().

{ return m_view.get(); }

view() [2/2]

template<typename Traits>

TrackingRecHit2DSOAView const* TrackingRecHit2DHeterogeneous< Traits >::view ( ) const

inline

Definition at line 58 of file TrackingRecHit2DHeterogeneous.h.

References TrackingRecHit2DHeterogeneous< Traits >::m_view.

{ return m_view.get(); }

Member Data Documentation

m_AverageGeometryStore

template<typename Traits>

unique_ptr<TrackingRecHit2DSOAView::AverageGeometry> TrackingRecHit2DHeterogeneous< Traits >::m_AverageGeometryStore

private

Definition at line 89 of file TrackingRecHit2DHeterogeneous.h.

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

m_hitsLayerStart

template<typename Traits>

uint32_t* TrackingRecHit2DHeterogeneous< Traits >::m_hitsLayerStart

private

Definition at line 102 of file TrackingRecHit2DHeterogeneous.h.

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

m_hitsModuleStart

template<typename Traits>

uint32_t const* TrackingRecHit2DHeterogeneous< Traits >::m_hitsModuleStart

private

Definition at line 96 of file TrackingRecHit2DHeterogeneous.h.

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

m_iphi

template<typename Traits>

int16_t* TrackingRecHit2DHeterogeneous< Traits >::m_iphi

private

Definition at line 103 of file TrackingRecHit2DHeterogeneous.h.

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

m_nHits

template<typename Traits>

uint32_t TrackingRecHit2DHeterogeneous< Traits >::m_nHits

private

Definition at line 93 of file TrackingRecHit2DHeterogeneous.h.

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

m_nMaxModules

template<typename Traits>

uint32_t TrackingRecHit2DHeterogeneous< Traits >::m_nMaxModules

private

Definition at line 98 of file TrackingRecHit2DHeterogeneous.h.

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

m_offsetBPIX2

template<typename Traits>

int32_t TrackingRecHit2DHeterogeneous< Traits >::m_offsetBPIX2

private

Definition at line 94 of file TrackingRecHit2DHeterogeneous.h.

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

m_phiBinner

template<typename Traits>

PhiBinner* TrackingRecHit2DHeterogeneous< Traits >::m_phiBinner

private

Definition at line 100 of file TrackingRecHit2DHeterogeneous.h.

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

m_phiBinnerStorage

template<typename Traits>

PhiBinner::index_type* TrackingRecHit2DHeterogeneous< Traits >::m_phiBinnerStorage

private

Definition at line 101 of file TrackingRecHit2DHeterogeneous.h.

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

m_PhiBinnerStore

template<typename Traits>

unique_ptr<TrackingRecHit2DSOAView::PhiBinner> TrackingRecHit2DHeterogeneous< Traits >::m_PhiBinnerStore

private

Definition at line 88 of file TrackingRecHit2DHeterogeneous.h.

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

m_store16

template<typename Traits>

unique_ptr<uint16_t[]> TrackingRecHit2DHeterogeneous< Traits >::m_store16

private

Definition at line 83 of file TrackingRecHit2DHeterogeneous.h.

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

m_store32

template<typename Traits>

unique_ptr<float[]> TrackingRecHit2DHeterogeneous< Traits >::m_store32

private

Definition at line 86 of file TrackingRecHit2DHeterogeneous.h.

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

m_view

template<typename Traits>

unique_ptr<TrackingRecHit2DSOAView> TrackingRecHit2DHeterogeneous< Traits >::m_view

private

Definition at line 91 of file TrackingRecHit2DHeterogeneous.h.

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

n16

template<typename Traits>

constexpr uint32_t TrackingRecHit2DHeterogeneous< Traits >::n16 = 4

staticprivate

Definition at line 81 of file TrackingRecHit2DHeterogeneous.h.

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

n32

template<typename Traits>

constexpr uint32_t TrackingRecHit2DHeterogeneous< Traits >::n32 = 10

staticprivate

Definition at line 82 of file TrackingRecHit2DHeterogeneous.h.

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