Inheritance diagram for EcalPhase2DigiToGPUProducer:

Public Member Functions
void	acquire (edm::Event const &event, edm::EventSetup const &setup, edm::WaitingTaskWithArenaHolder holder) override

	EcalPhase2DigiToGPUProducer (const edm::ParameterSet &ps)

void	produce (edm::Event &evt, edm::EventSetup const &setup) override

	~EcalPhase2DigiToGPUProducer () override=default

Public Member Functions inherited from edm::stream::EDProducer< edm::ExternalWork >
	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 EDProducer &	operator= (const EDProducer &)=delete

Static Public Member Functions
static void	fillDescriptions (edm::ConfigurationDescriptions &descriptions)

Private Attributes
cms::cuda::ContextState	cudaState_

const edm::EDGetTokenT< EBDigiCollectionPh2 >	digiCollectionToken_

ecal::DigisCollection<::calo::common::DevStoragePolicy >	digis_

const edm::EDPutTokenT< cms::cuda::Product< ecal::DigisCollection< calo::common::DevStoragePolicy > > >	digisCollectionToken_

uint32_t	size_

Additional Inherited Members
Public Types inherited from edm::stream::EDProducer< edm::ExternalWork >
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 15 of file EcalPhase2DigiToGPUProducer.cc.

Constructor & Destructor Documentation

◆ EcalPhase2DigiToGPUProducer()

EcalPhase2DigiToGPUProducer::EcalPhase2DigiToGPUProducer ( const edm::ParameterSet & ps )

explicit

Definition at line 44 of file EcalPhase2DigiToGPUProducer.cc.

     : digiCollectionToken_(consumes<EBDigiCollectionPh2>(ps.getParameter<edm::InputTag>("BarrelDigis"))),
       digisCollectionToken_(produces<cms::cuda::Product<ecal::DigisCollection<calo::common::DevStoragePolicy>>>(
           ps.getParameter<std::string>("digisLabelEB"))) {}

◆ ~EcalPhase2DigiToGPUProducer()

EcalPhase2DigiToGPUProducer::~EcalPhase2DigiToGPUProducer ( )

overridedefault

Member Function Documentation

◆ acquire()

void EcalPhase2DigiToGPUProducer::acquire	(	edm::Event const &	event,
		edm::EventSetup const &	setup,
		edm::WaitingTaskWithArenaHolder	holder
	)

override

Definition at line 49 of file EcalPhase2DigiToGPUProducer.cc.

References cudaCheck, cudaState_, digiCollectionToken_, digis_, mps_fire::i, EcalDataFrame_Ph2::MAXSAMPLES, eostools::move(), PresampleTask_cfi::nSamples, Digi_cff::pdigi, EcalLiteDTUSample::raw(), ecalGpuTask_cfi::sample, and size_.

                                                                                 {
   cms::cuda::ScopedContextAcquire ctx{event.streamID(), std::move(holder), cudaState_};
 
   //input data from event
   const auto& pdigis = event.get(digiCollectionToken_);
 
   size_ = pdigis.size();
 
   digis_.size = size_;
   //allocate device pointers for output
   digis_.ids = cms::cuda::make_device_unique<uint32_t[]>(size_, ctx.stream());
   digis_.data = cms::cuda::make_device_unique<uint16_t[]>(size_ * EcalDataFrame_Ph2::MAXSAMPLES, ctx.stream());
 
   //allocate host pointers for holding product data and id vectors
   auto idstmp = cms::cuda::make_host_unique<uint32_t[]>(size_, ctx.stream());
   auto datatmp = cms::cuda::make_host_unique<uint16_t[]>(size_ * EcalDataFrame_Ph2::MAXSAMPLES, ctx.stream());
 
   //iterate over digis
   uint32_t i = 0;
   for (const auto& pdigi : pdigis) {
     const int nSamples = pdigi.size();
     //assign id to output vector
     idstmp.get()[i] = pdigi.id();
     //iterate over sample in digi
     for (int sample = 0; sample < nSamples; ++sample) {
       //get samples from input digi
       EcalLiteDTUSample thisSample = pdigi[sample];
       //assign adc data to output
       datatmp.get()[i * nSamples + sample] = thisSample.raw();
     }
     ++i;
   }
 
   //copy output vectors into member variable device pointers for the output struct
 
   cudaCheck(
       cudaMemcpyAsync(digis_.ids.get(), idstmp.get(), size_ * sizeof(uint32_t), cudaMemcpyHostToDevice, ctx.stream()));
   cudaCheck(cudaMemcpyAsync(digis_.data.get(),
                             datatmp.get(),
                             size_ * EcalDataFrame_Ph2::MAXSAMPLES * sizeof(uint16_t),
                             cudaMemcpyHostToDevice,
                             ctx.stream()));
 }

◆ fillDescriptions()

void EcalPhase2DigiToGPUProducer::fillDescriptions ( edm::ConfigurationDescriptions & descriptions )

static

Definition at line 35 of file EcalPhase2DigiToGPUProducer.cc.

References edm::ConfigurationDescriptions::addWithDefaultLabel(), submitPVResolutionJobs::desc, HLT_2022v14_cff::InputTag, and AlCaHLTBitMon_QueryRunRegistry::string.

                                                                                              {
   edm::ParameterSetDescription desc;
 
   desc.add<edm::InputTag>("BarrelDigis", edm::InputTag("simEcalUnsuppressedDigis", ""));
   desc.add<std::string>("digisLabelEB", "ebDigis");
 
   descriptions.addWithDefaultLabel(desc);
 }

◆ produce()

void EcalPhase2DigiToGPUProducer::produce	(	edm::Event &	evt,
		edm::EventSetup const &	setup
	)

override

Definition at line 95 of file EcalPhase2DigiToGPUProducer.cc.

References cudaState_, digis_, digisCollectionToken_, and eostools::move().

                                                                                      {
   //get cuda context state for producer
   cms::cuda::ScopedContextProduce ctx{cudaState_};
 
   //emplace output in the context
   ctx.emplace(event, digisCollectionToken_, std::move(digis_));
 }