Inheritance diagram for SiPixelRecHitSoAFromCUDAT< TrackerTraits >:

Public Types
using	HitsOnDevice = TrackingRecHitSoADevice< TrackerTraits >

using	HitsOnHost = TrackingRecHitSoAHost< TrackerTraits >

using	HMSstorage = HostProduct< uint32_t[]>

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

Public Member Functions
	SiPixelRecHitSoAFromCUDAT (const edm::ParameterSet &iConfig)

	~SiPixelRecHitSoAFromCUDAT () 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 (edm::Event const &iEvent, edm::EventSetup const &iSetup, edm::WaitingTaskWithArenaHolder waitingTaskHolder) override

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

Private Attributes
HitsOnHost	hits_h_

const edm::EDPutTokenT< HitsOnHost >	hitsPutTokenCPU_

const edm::EDGetTokenT< cms::cuda::Product< HitsOnDevice > >	hitsTokenGPU_

const edm::EDPutTokenT< HMSstorage >	hostPutToken_

uint32_t	nHits_

Detailed Description

template<typename TrackerTraits>
class SiPixelRecHitSoAFromCUDAT< TrackerTraits >

Definition at line 29 of file SiPixelRecHitSoAFromCUDA.cc.

Member Typedef Documentation

◆ HitsOnDevice

template<typename TrackerTraits >

using SiPixelRecHitSoAFromCUDAT< TrackerTraits >::HitsOnDevice = TrackingRecHitSoADevice<TrackerTraits>

Definition at line 37 of file SiPixelRecHitSoAFromCUDA.cc.

◆ HitsOnHost

template<typename TrackerTraits >

using SiPixelRecHitSoAFromCUDAT< TrackerTraits >::HitsOnHost = TrackingRecHitSoAHost<TrackerTraits>

Definition at line 36 of file SiPixelRecHitSoAFromCUDA.cc.

◆ HMSstorage

template<typename TrackerTraits >

using SiPixelRecHitSoAFromCUDAT< TrackerTraits >::HMSstorage = HostProduct<uint32_t[]>

Definition at line 35 of file SiPixelRecHitSoAFromCUDA.cc.

Constructor & Destructor Documentation

◆ SiPixelRecHitSoAFromCUDAT()

template<typename TrackerTraits >

SiPixelRecHitSoAFromCUDAT< TrackerTraits >::SiPixelRecHitSoAFromCUDAT ( const edm::ParameterSet & iConfig )

explicit

Definition at line 54 of file SiPixelRecHitSoAFromCUDA.cc.

     : hitsTokenGPU_(consumes(iConfig.getParameter<edm::InputTag>("pixelRecHitSrc"))),
       hitsPutTokenCPU_(produces<HitsOnHost>()),
       hostPutToken_(produces<HMSstorage>()) {}

◆ ~SiPixelRecHitSoAFromCUDAT()

template<typename TrackerTraits >

SiPixelRecHitSoAFromCUDAT< TrackerTraits >::~SiPixelRecHitSoAFromCUDAT ( )

overridedefault

Member Function Documentation

◆ acquire()

template<typename TrackerTraits >

void SiPixelRecHitSoAFromCUDAT< TrackerTraits >::acquire	(	edm::Event const &	iEvent,
		edm::EventSetup const &	iSetup,
		edm::WaitingTaskWithArenaHolder	waitingTaskHolder
	)

overrideprivate

Definition at line 68 of file SiPixelRecHitSoAFromCUDA.cc.

References cudaCheck, iEvent, LogDebug, and eostools::move().

                                                                                                         {
   cms::cuda::Product<HitsOnDevice> const& inputDataWrapped = iEvent.get(hitsTokenGPU_);
   cms::cuda::ScopedContextAcquire ctx{inputDataWrapped, std::move(waitingTaskHolder)};
   auto const& inputData = ctx.get(inputDataWrapped);
 
   nHits_ = inputData.nHits();
   hits_h_ = HitsOnHost(nHits_, ctx.stream());
   cudaCheck(cudaMemcpyAsync(hits_h_.buffer().get(),
                             inputData.const_buffer().get(),
                             inputData.bufferSize(),
                             cudaMemcpyDeviceToHost,
                             ctx.stream()));  // Copy data from Device to Host
   LogDebug("SiPixelRecHitSoAFromCUDA") << "copying to cpu SoA" << inputData.nHits() << " Hits";
 }

◆ fillDescriptions()

template<typename TrackerTraits >

void SiPixelRecHitSoAFromCUDAT< TrackerTraits >::fillDescriptions ( edm::ConfigurationDescriptions & descriptions )

static

Definition at line 60 of file SiPixelRecHitSoAFromCUDA.cc.

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

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

◆ produce()

template<typename TrackerTraits >

void SiPixelRecHitSoAFromCUDAT< TrackerTraits >::produce	(	edm::Event &	iEvent,
		edm::EventSetup const &	iSetup
	)

overrideprivate

Definition at line 86 of file SiPixelRecHitSoAFromCUDA.cc.

References filterCSVwithJSON::copy, iEvent, eostools::move(), and phase1PixelTopology::numberOfModules.

                                                                                                 {
   auto hmsp = std::make_unique<uint32_t[]>(TrackerTraits::numberOfModules + 1);
 
   if (nHits_ > 0)
     std::copy(hits_h_.view().hitsModuleStart().begin(), hits_h_.view().hitsModuleStart().end(), hmsp.get());
 
   iEvent.emplace(hostPutToken_, std::move(hmsp));
   iEvent.emplace(hitsPutTokenCPU_, std::move(hits_h_));
 }