CMS 3D CMS Logo

List of all members | Public Member Functions | Private Member Functions | Private Attributes
HEFRecHitGPU Class Reference
Inheritance diagram for HEFRecHitGPU:
edm::stream::EDProducer<>

Public Member Functions

void beginRun (edm::Run const &, edm::EventSetup const &) override
 
 HEFRecHitGPU (const edm::ParameterSet &ps)
 
void produce (edm::Event &, const edm::EventSetup &) override
 
 ~HEFRecHitGPU () override
 
- Public Member Functions inherited from edm::stream::EDProducer<>
 EDProducer ()=default
 
 EDProducer (const EDProducer &)=delete
 
bool hasAbilityToProduceInBeginLumis () const final
 
bool hasAbilityToProduceInBeginProcessBlocks () const final
 
bool hasAbilityToProduceInBeginRuns () const final
 
bool hasAbilityToProduceInEndLumis () const final
 
bool hasAbilityToProduceInEndProcessBlocks () const final
 
bool hasAbilityToProduceInEndRuns () const final
 
const EDProduceroperator= (const EDProducer &)=delete
 

Private Member Functions

std::string assert_error_message_ (std::string, const size_t &, const size_t &)
 
void assert_sizes_constants_ (const HGCConstantVectorData &)
 
void convert_collection_data_to_soa_ (const uint32_t &, const HGChefUncalibratedRecHitCollection &)
 
void convert_constant_data_ (KernelConstantData< HGChefUncalibRecHitConstantData > *)
 

Private Attributes

HGChefUncalibRecHitConstantData cdata_
 
HGCUncalibRecHitDevice d_uncalib_
 
HGCUncalibRecHitHost< HGChefUncalibratedRecHitCollectionh_uncalib_
 
KernelConstantData< HGChefUncalibRecHitConstantData > * kcdata_
 
HGCRecHitGPUProduct prod_
 
edm::EDPutTokenT< cms::cuda::Product< HGCRecHitGPUProduct > > recHitGPUToken_
 
std::unique_ptr< HGChefRecHitCollectionrechits_
 
std::unique_ptr< hgcal::RecHitToolstools_
 
edm::EDGetTokenT< HGChefUncalibratedRecHitCollectionuncalibRecHitCPUToken_
 
HGCConstantVectorData vdata_
 

Additional Inherited Members

- Public Types inherited from edm::stream::EDProducer<>
using CacheTypes = CacheContexts< T... >
 
using GlobalCache = typename CacheTypes::GlobalCache
 
using HasAbility = AbilityChecker< T... >
 
using InputProcessBlockCache = typename CacheTypes::InputProcessBlockCache
 
using LuminosityBlockCache = typename CacheTypes::LuminosityBlockCache
 
using LuminosityBlockContext = LuminosityBlockContextT< LuminosityBlockCache, RunCache, GlobalCache >
 
using LuminosityBlockSummaryCache = typename CacheTypes::LuminosityBlockSummaryCache
 
using RunCache = typename CacheTypes::RunCache
 
using RunContext = RunContextT< RunCache, GlobalCache >
 
using RunSummaryCache = typename CacheTypes::RunSummaryCache
 

Detailed Description

Definition at line 24 of file HEFRecHitGPU.cc.

Constructor & Destructor Documentation

◆ HEFRecHitGPU()

HEFRecHitGPU::HEFRecHitGPU ( const edm::ParameterSet ps)
explicit

Definition at line 60 of file HEFRecHitGPU.cc.

61  : uncalibRecHitCPUToken_{consumes<HGCUncalibratedRecHitCollection>(
62  ps.getParameter<edm::InputTag>("HGCHEFUncalibRecHitsTok"))},
63  recHitGPUToken_{produces<cms::cuda::Product<HGCRecHitGPUProduct>>()} {
64  cdata_.keV2DIGI_ = ps.getParameter<double>("HGCHEF_keV2DIGI");
65  cdata_.xmin_ = ps.getParameter<double>("minValSiPar"); //float
66  cdata_.xmax_ = ps.getParameter<double>("maxValSiPar"); //float
67  cdata_.aterm_ = ps.getParameter<double>("noiseSiPar"); //float
68  cdata_.cterm_ = ps.getParameter<double>("constSiPar"); //float
69  vdata_.fCPerMIP_ = ps.getParameter<std::vector<double>>("HGCHEF_fCPerMIP");
70  vdata_.cce_ = ps.getParameter<edm::ParameterSet>("HGCHEF_cce").getParameter<std::vector<double>>("values");
71  vdata_.noise_fC_ = ps.getParameter<edm::ParameterSet>("HGCHEF_noise_fC").getParameter<std::vector<double>>("values");
72  vdata_.rcorr_ = ps.getParameter<std::vector<double>>("rcorr");
73  vdata_.weights_ = ps.getParameter<std::vector<double>>("weights");
75  cdata_.layerOffset_ = 28;
77 
80 
81  tools_ = std::make_unique<hgcal::RecHitTools>();
82 }

References edm::ParameterSet::getParameter().

◆ ~HEFRecHitGPU()

HEFRecHitGPU::~HEFRecHitGPU ( )
override

Definition at line 84 of file HEFRecHitGPU.cc.

84 { delete kcdata_; }

References kcdata_.

Member Function Documentation

◆ assert_error_message_()

std::string HEFRecHitGPU::assert_error_message_ ( std::string  var,
const size_t &  s1,
const size_t &  s2 
)
private

Definition at line 86 of file HEFRecHitGPU.cc.

86  {
87  std::string str1 = "The '";
88  std::string str2 = "' array must be of size ";
89  std::string str3 = " to hold the configuration data, but is of size ";
90  return str1 + var + str2 + std::to_string(s1) + str3 + std::to_string(s2);
91 }

References AlCaHLTBitMon_QueryRunRegistry::string, and trigObjTnPSource_cfi::var.

Referenced by assert_sizes_constants_().

◆ assert_sizes_constants_()

void HEFRecHitGPU::assert_sizes_constants_ ( const HGCConstantVectorData vd)
private

Definition at line 93 of file HEFRecHitGPU.cc.

References assert_error_message_(), HGCConstantVectorData::cce_, HGCConstantVectorData::fCPerMIP_, HGChefUncalibRecHitConstantData::hef_cce, HGChefUncalibRecHitConstantData::hef_fCPerMIP, HGChefUncalibRecHitConstantData::hef_noise_fC, HGChefUncalibRecHitConstantData::hef_rcorr, HGChefUncalibRecHitConstantData::hef_weights, HGCConstantVectorData::noise_fC_, HGCConstantVectorData::rcorr_, vdata_, and HGCConstantVectorData::weights_.

◆ beginRun()

void HEFRecHitGPU::beginRun ( edm::Run const &  ,
edm::EventSetup const &  setup 
)
override

Definition at line 111 of file HEFRecHitGPU.cc.

111 {}

◆ convert_collection_data_to_soa_()

void HEFRecHitGPU::convert_collection_data_to_soa_ ( const uint32_t &  ,
const HGChefUncalibratedRecHitCollection  
)
private

◆ convert_constant_data_()

void HEFRecHitGPU::convert_constant_data_ ( KernelConstantData< HGChefUncalibRecHitConstantData > *  kcdata)
private

Definition at line 133 of file HEFRecHitGPU.cc.

133  {
134  for (size_t i = 0; i < kcdata->vdata_.fCPerMIP_.size(); ++i)
135  kcdata->data_.fCPerMIP_[i] = kcdata->vdata_.fCPerMIP_[i];
136  for (size_t i = 0; i < kcdata->vdata_.cce_.size(); ++i)
137  kcdata->data_.cce_[i] = kcdata->vdata_.cce_[i];
138  for (size_t i = 0; i < kcdata->vdata_.noise_fC_.size(); ++i)
139  kcdata->data_.noise_fC_[i] = kcdata->vdata_.noise_fC_[i];
140  for (size_t i = 0; i < kcdata->vdata_.rcorr_.size(); ++i)
141  kcdata->data_.rcorr_[i] = kcdata->vdata_.rcorr_[i];
142  for (size_t i = 0; i < kcdata->vdata_.weights_.size(); ++i)
143  kcdata->data_.weights_[i] = kcdata->vdata_.weights_[i];
144 }

References HGCConstantVectorData::cce_, HGChefUncalibRecHitConstantData::cce_, KernelConstantData< T >::data_, HGCConstantVectorData::fCPerMIP_, HGChefUncalibRecHitConstantData::fCPerMIP_, cms::cuda::for(), mps_fire::i, HGCConstantVectorData::noise_fC_, HGChefUncalibRecHitConstantData::noise_fC_, HGCConstantVectorData::rcorr_, HGChefUncalibRecHitConstantData::rcorr_, KernelConstantData< T >::vdata_, HGCConstantVectorData::weights_, and HGChefUncalibRecHitConstantData::weights_.

◆ produce()

void HEFRecHitGPU::produce ( edm::Event event,
const edm::EventSetup setup 
)
override

Definition at line 113 of file HEFRecHitGPU.cc.

113  {
114  cms::cuda::ScopedContextProduce ctx{event.streamID()};
115 
116  const auto &hits = event.get(uncalibRecHitCPUToken_);
117  unsigned int nhits(hits.size());
118  rechits_ = std::make_unique<HGCRecHitCollection>();
119 
120  if (nhits == 0)
121  edm::LogError("HEFRecHitGPU") << "WARNING: no input hits!";
122 
123  prod_ = HGCRecHitGPUProduct(nhits, ctx.stream());
124  d_uncalib_ = HGCUncalibRecHitDevice(nhits, ctx.stream());
126 
128  km.run_kernels(kcdata_, ctx.stream());
129 
130  ctx.emplace(event, recHitGPUToken_, std::move(prod_));
131 }

References d_uncalib_, HGCUncalibRecHitDevice::get(), HGCRecHitGPUProduct::get(), h_uncalib_, hfClusterShapes_cfi::hits, kcdata_, eostools::move(), nhits, prod_, recHitGPUToken_, rechits_, KernelManagerHGCalRecHit::run_kernels(), and uncalibRecHitCPUToken_.

Member Data Documentation

◆ cdata_

HGChefUncalibRecHitConstantData HEFRecHitGPU::cdata_
private

Definition at line 39 of file HEFRecHitGPU.cc.

◆ d_uncalib_

HGCUncalibRecHitDevice HEFRecHitGPU::d_uncalib_
private

Definition at line 54 of file HEFRecHitGPU.cc.

Referenced by produce().

◆ h_uncalib_

HGCUncalibRecHitHost<HGChefUncalibratedRecHitCollection> HEFRecHitGPU::h_uncalib_
private

Definition at line 55 of file HEFRecHitGPU.cc.

Referenced by produce().

◆ kcdata_

KernelConstantData<HGChefUncalibRecHitConstantData>* HEFRecHitGPU::kcdata_
private

Definition at line 57 of file HEFRecHitGPU.cc.

Referenced by produce(), and ~HEFRecHitGPU().

◆ prod_

HGCRecHitGPUProduct HEFRecHitGPU::prod_
private

Definition at line 53 of file HEFRecHitGPU.cc.

Referenced by produce().

◆ recHitGPUToken_

edm::EDPutTokenT<cms::cuda::Product<HGCRecHitGPUProduct> > HEFRecHitGPU::recHitGPUToken_
private

Definition at line 34 of file HEFRecHitGPU.cc.

Referenced by produce().

◆ rechits_

std::unique_ptr<HGChefRecHitCollection> HEFRecHitGPU::rechits_
private

Definition at line 36 of file HEFRecHitGPU.cc.

Referenced by produce().

◆ tools_

std::unique_ptr<hgcal::RecHitTools> HEFRecHitGPU::tools_
private

Definition at line 47 of file HEFRecHitGPU.cc.

◆ uncalibRecHitCPUToken_

edm::EDGetTokenT<HGChefUncalibratedRecHitCollection> HEFRecHitGPU::uncalibRecHitCPUToken_
private

Definition at line 33 of file HEFRecHitGPU.cc.

Referenced by produce().

◆ vdata_

HGCConstantVectorData HEFRecHitGPU::vdata_
private

Definition at line 40 of file HEFRecHitGPU.cc.

Referenced by assert_sizes_constants_().

HGCUncalibRecHitHost
Definition: HGCUncalibRecHitHost.h:12
mps_fire.i
i
Definition: mps_fire.py:428
HGChefUncalibRecHitConstantData::noise_fC_
double noise_fC_[hef_noise_fC]
Definition: HGCUncalibRecHitsToRecHitsConstants.h:48
hfClusterShapes_cfi.hits
hits
Definition: hfClusterShapes_cfi.py:5
KernelConstantData::vdata_
HGCConstantVectorData vdata_
Definition: KernelManagerHGCalRecHit.h:30
KernelConstantData::data_
T data_
Definition: KernelManagerHGCalRecHit.h:29
cms::cuda::ScopedContextProduce
Definition: ScopedContext.h:149
HEFRecHitGPU::d_uncalib_
HGCUncalibRecHitDevice d_uncalib_
Definition: HEFRecHitGPU.cc:54
HGChefUncalibRecHitConstantData::uncalib2GeV_
double uncalib2GeV_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:53
HEFRecHitGPU::recHitGPUToken_
edm::EDPutTokenT< cms::cuda::Product< HGCRecHitGPUProduct > > recHitGPUToken_
Definition: HEFRecHitGPU.cc:34
HGCRecHitGPUProduct
Definition: HGCRecHitGPUProduct.h:12
HGChefUncalibRecHitConstantData::hef_rcorr
static constexpr size_t hef_rcorr
Definition: HGCUncalibRecHitsToRecHitsConstants.h:43
KernelManagerHGCalRecHit
Definition: KernelManagerHGCalRecHit.h:33
HEFRecHitGPU::assert_sizes_constants_
void assert_sizes_constants_(const HGCConstantVectorData &)
Definition: HEFRecHitGPU.cc:93
HEFRecHitGPU::convert_constant_data_
void convert_constant_data_(KernelConstantData< HGChefUncalibRecHitConstantData > *)
Definition: HEFRecHitGPU.cc:133
trigObjTnPSource_cfi.var
var
Definition: trigObjTnPSource_cfi.py:21
HEFRecHitGPU::h_uncalib_
HGCUncalibRecHitHost< HGChefUncalibratedRecHitCollection > h_uncalib_
Definition: HEFRecHitGPU.cc:55
HGCUncalibRecHitDevice
Definition: HGCUncalibRecHitDevice.h:11
HGChefUncalibRecHitConstantData::layerOffset_
std::int32_t layerOffset_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:58
HGCConstantVectorData::fCPerMIP_
std::vector< double > fCPerMIP_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:9
HEFRecHitGPU::kcdata_
KernelConstantData< HGChefUncalibRecHitConstantData > * kcdata_
Definition: HEFRecHitGPU.cc:57
nhits
Definition: HIMultiTrackSelector.h:42
HGChefUncalibRecHitConstantData::weights_
double weights_[hef_weights]
Definition: HGCUncalibRecHitsToRecHitsConstants.h:50
HEFRecHitGPU::rechits_
std::unique_ptr< HGChefRecHitCollection > rechits_
Definition: HEFRecHitGPU.cc:36
HGChefUncalibRecHitConstantData::hef_fCPerMIP
static constexpr size_t hef_fCPerMIP
Definition: HGCUncalibRecHitsToRecHitsConstants.h:40
edm::ParameterSet
Definition: ParameterSet.h:47
HGChefUncalibRecHitConstantData::xmin_
float xmin_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:54
HGCConstantVectorData::rcorr_
std::vector< double > rcorr_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:12
edm::LogError
Log< level::Error, false > LogError
Definition: MessageLogger.h:123
cms::cuda::for
for(int i=first, nt=offsets[nh];i< nt;i+=gridDim.x *blockDim.x)
Definition: HistoContainer.h:15
AlCaHLTBitMon_QueryRunRegistry.string
string string
Definition: AlCaHLTBitMon_QueryRunRegistry.py:256
HGChefUncalibRecHitConstantData::hef_cce
static constexpr size_t hef_cce
Definition: HGCUncalibRecHitsToRecHitsConstants.h:41
HGCConstantVectorData::cce_
std::vector< double > cce_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:10
HGCRecHitGPUProduct::get
HGCRecHitSoA get()
Definition: HGCRecHitGPUProduct.h:27
KernelManagerHGCalRecHit::run_kernels
void run_kernels(const KernelConstantData< HGCeeUncalibRecHitConstantData > *, const cudaStream_t &)
HGChefUncalibRecHitConstantData::rcorr_
double rcorr_[hef_rcorr]
Definition: HGCUncalibRecHitsToRecHitsConstants.h:49
eostools.move
def move(src, dest)
Definition: eostools.py:511
HGCUncalibRecHitDevice::get
HGCUncalibRecHitSoA get() const
Definition: HGCUncalibRecHitDevice.h:23
HEFRecHitGPU::prod_
HGCRecHitGPUProduct prod_
Definition: HEFRecHitGPU.cc:53
HGChefUncalibRecHitConstantData::hef_weights
static constexpr size_t hef_weights
Definition: HGCUncalibRecHitsToRecHitsConstants.h:44
HGChefUncalibRecHitConstantData::hef_noise_fC
static constexpr size_t hef_noise_fC
Definition: HGCUncalibRecHitsToRecHitsConstants.h:42
HEFRecHitGPU::assert_error_message_
std::string assert_error_message_(std::string, const size_t &, const size_t &)
Definition: HEFRecHitGPU.cc:86
edm::ParameterSet::getParameter
T getParameter(std::string const &) const
Definition: ParameterSet.h:303
HGChefUncalibRecHitConstantData::aterm_
float aterm_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:56
HGChefUncalibRecHitConstantData::fCPerMIP_
double fCPerMIP_[hef_fCPerMIP]
Definition: HGCUncalibRecHitsToRecHitsConstants.h:46
KernelConstantData< HGChefUncalibRecHitConstantData >
HEFRecHitGPU::tools_
std::unique_ptr< hgcal::RecHitTools > tools_
Definition: HEFRecHitGPU.cc:47
HEFRecHitGPU::cdata_
HGChefUncalibRecHitConstantData cdata_
Definition: HEFRecHitGPU.cc:39
HEFRecHitGPU::uncalibRecHitCPUToken_
edm::EDGetTokenT< HGChefUncalibratedRecHitCollection > uncalibRecHitCPUToken_
Definition: HEFRecHitGPU.cc:33
HGChefUncalibRecHitConstantData::cce_
double cce_[hef_cce]
Definition: HGCUncalibRecHitsToRecHitsConstants.h:47
HGCConstantVectorData::weights_
std::vector< double > weights_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:13
event
Definition: event.py:1
HGCConstantVectorData::noise_fC_
std::vector< double > noise_fC_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:11
HGChefUncalibRecHitConstantData::keV2DIGI_
double keV2DIGI_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:52
edm::Log
Definition: MessageLogger.h:70
edm::InputTag
Definition: InputTag.h:15
HEFRecHitGPU::vdata_
HGCConstantVectorData vdata_
Definition: HEFRecHitGPU.cc:40
HGChefUncalibRecHitConstantData::xmax_
float xmax_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:55
MillePedeFileConverter_cfg.e
e
Definition: MillePedeFileConverter_cfg.py:37
HGChefUncalibRecHitConstantData::cterm_
float cterm_
Definition: HGCUncalibRecHitsToRecHitsConstants.h:57