Inheritance diagram for EcalPhase2DigiToGPUProducer:

Public Member Functions
	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<>
	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
const edm::EDGetTokenT< EBDigiCollectionPh2 >	digiCollectionToken_

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

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 15 of file EcalPhase2DigiToGPUProducer.cc.

Constructor & Destructor Documentation

◆ EcalPhase2DigiToGPUProducer()

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

explicit

Definition at line 38 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

◆ fillDescriptions()

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

static

Definition at line 29 of file EcalPhase2DigiToGPUProducer.cc.

References edm::ConfigurationDescriptions::addWithDefaultLabel(), submitPVResolutionJobs::desc, ProducerED_cfi::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 43 of file EcalPhase2DigiToGPUProducer.cc.

References cudaCheck, ecal::DigisCollection< StoragePolicy >::data, digiCollectionToken_, digisCollectionToken_, cms::cuda::impl::ScopedContextGetterBase::get(), mps_fire::i, ecal::DigisCollection< StoragePolicy >::ids, EcalDataFrame_Ph2::MAXSAMPLES, eostools::move(), PresampleTask_cfi::nSamples, redigi_cff::pdigi, EcalLiteDTUSample::raw(), ecalGpuTask_cfi::sample, and findQualityFiles::size.

                                                                                      {
   cms::cuda::ScopedContextProduce ctx{event.streamID()};
 
   //input data from event
   const auto& pdigis = event.get(digiCollectionToken_);
 
   const uint32_t size = pdigis.size();
 
   ecal::DigisCollection<::calo::common::DevStoragePolicy> digis;
   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()));
 
   //emplace output in the context
   ctx.emplace(event, digisCollectionToken_, std::move(digis));
 }