SiPixelDigisSoAFromCUDA Class Reference

Inheritance diagram for SiPixelDigisSoAFromCUDA:

Public Member Functions
	SiPixelDigisSoAFromCUDA (const edm::ParameterSet &iConfig)
	~SiPixelDigisSoAFromCUDA () 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 Member Functions
void	acquire (const edm::Event &iEvent, const edm::EventSetup &iSetup, edm::WaitingTaskWithArenaHolder waitingTaskHolder) override
void	produce (edm::Event &iEvent, const edm::EventSetup &iSetup) override

Private Attributes
edm::EDGetTokenT< cms::cuda::Product< SiPixelDigisCUDA > >	digiGetToken_
edm::EDPutTokenT< SiPixelDigisSoA >	digiPutToken_
cms::cuda::PortableHostCollection< SiPixelDigisSoALayout<> >	digis_h_
int	nDigis_

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 SiPixelDigisSoAFromCUDA.cc.

Constructor & Destructor Documentation

SiPixelDigisSoAFromCUDA()

SiPixelDigisSoAFromCUDA::SiPixelDigisSoAFromCUDA ( const edm::ParameterSet &  iConfig )

explicit

Definition at line 36 of file SiPixelDigisSoAFromCUDA.cc.

    : digiGetToken_(consumes<cms::cuda::Product<SiPixelDigisCUDA>>(iConfig.getParameter<edm::InputTag>("src"))),
      digiPutToken_(produces<SiPixelDigisSoA>()) {}

~SiPixelDigisSoAFromCUDA()

SiPixelDigisSoAFromCUDA::~SiPixelDigisSoAFromCUDA ( )

overridedefault

Member Function Documentation

acquire()

void SiPixelDigisSoAFromCUDA::acquire ( const edm::Event &  iEvent, const edm::EventSetup &  iSetup, edm::WaitingTaskWithArenaHolder  waitingTaskHolder  )

overrideprivate

Definition at line 46 of file SiPixelDigisSoAFromCUDA.cc.

References cms::cuda::PortableHostCollection< T >::buffer(), cudaCheck, digiGetToken_, digis_h_, iEvent, eostools::move(), and nDigis_.

                                                                                       {
  // Do the transfer in a CUDA stream parallel to the computation CUDA stream
  cms::cuda::ScopedContextAcquire ctx{iEvent.streamID(), std::move(waitingTaskHolder)};

  const auto& digis_d = ctx.get(iEvent, digiGetToken_);

  nDigis_ = digis_d.nDigis();
  nDigis_ = digis_d.nDigis();
  digis_h_ = cms::cuda::PortableHostCollection<SiPixelDigisSoALayout<>>(digis_d.view().metadata().size(), ctx.stream());
  cudaCheck(cudaMemcpyAsync(digis_h_.buffer().get(),
                            digis_d.const_buffer().get(),
                            digis_d.bufferSize(),
                            cudaMemcpyDeviceToHost,
                            ctx.stream()));
}

fillDescriptions()

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

static

Definition at line 40 of file SiPixelDigisSoAFromCUDA.cc.

References edm::ConfigurationDescriptions::addWithDefaultLabel(), submitPVResolutionJobs::desc, and ProducerED_cfi::InputTag.

                                                                                         {
  edm::ParameterSetDescription desc;
  desc.add<edm::InputTag>("src", edm::InputTag("siPixelClustersCUDA"));
  descriptions.addWithDefaultLabel(desc);
}

produce()

void SiPixelDigisSoAFromCUDA::produce ( edm::Event &  iEvent, const edm::EventSetup &  iSetup  )

overrideprivate

Definition at line 64 of file SiPixelDigisSoAFromCUDA.cc.

References digiPutToken_, digis_h_, iEvent, nDigis_, and cms::cuda::PortableHostCollection< T >::view().

                                                                                   {
  iEvent.emplace(digiPutToken_,
                 nDigis_,
                 digis_h_.view().pdigi(),
                 digis_h_.view().rawIdArr(),
                 digis_h_.view().adc(),
                 digis_h_.view().clus());
}

Member Data Documentation

digiGetToken_

edm::EDGetTokenT<cms::cuda::Product<SiPixelDigisCUDA> > SiPixelDigisSoAFromCUDA::digiGetToken_

private

Definition at line 28 of file SiPixelDigisSoAFromCUDA.cc.

Referenced by acquire().

digiPutToken_

edm::EDPutTokenT<SiPixelDigisSoA> SiPixelDigisSoAFromCUDA::digiPutToken_

private

Definition at line 29 of file SiPixelDigisSoAFromCUDA.cc.

Referenced by produce().

digis_h_

cms::cuda::PortableHostCollection<SiPixelDigisSoALayout<> > SiPixelDigisSoAFromCUDA::digis_h_

private

Definition at line 31 of file SiPixelDigisSoAFromCUDA.cc.

Referenced by acquire(), and produce().

nDigis_

int SiPixelDigisSoAFromCUDA::nDigis_

private

Definition at line 33 of file SiPixelDigisSoAFromCUDA.cc.

Referenced by acquire(), and produce().