SiPixelDigisCUDA Class Reference

#include <SiPixelDigisCUDA.h>

Public Types
using	StoreType = uint16_t

Public Member Functions
cms::cuda::host::unique_ptr< StoreType[]>	copyAllToHostAsync (cudaStream_t stream) const
uint32_t	nDigis () const
uint32_t	nModules () const
SiPixelDigisCUDA &	operator= (const SiPixelDigisCUDA &)=delete
SiPixelDigisCUDA &	operator= (SiPixelDigisCUDA &&)=default
void	setNModulesDigis (uint32_t nModules, uint32_t nDigis)
	SiPixelDigisCUDA ()=default
	SiPixelDigisCUDA (size_t maxFedWords, cudaStream_t stream)
	SiPixelDigisCUDA (const SiPixelDigisCUDA &)=delete
	SiPixelDigisCUDA (SiPixelDigisCUDA &&)=default
SiPixelDigisCUDASOAView	view ()
SiPixelDigisCUDASOAView const	view () const
	~SiPixelDigisCUDA ()=default

Private Attributes
cms::cuda::device::unique_ptr< StoreType[]>	m_store
SiPixelDigisCUDASOAView	m_view
uint32_t	nDigis_h = 0
uint32_t	nModules_h = 0

Detailed Description

Definition at line 11 of file SiPixelDigisCUDA.h.

Member Typedef Documentation

StoreType

using SiPixelDigisCUDA::StoreType = uint16_t

Definition at line 13 of file SiPixelDigisCUDA.h.

Constructor & Destructor Documentation

SiPixelDigisCUDA() [1/4]

SiPixelDigisCUDA::SiPixelDigisCUDA ( )

default

SiPixelDigisCUDA() [2/4]

SiPixelDigisCUDA::SiPixelDigisCUDA ( size_t  maxFedWords, cudaStream_t  stream  )

explicit

Definition at line 8 of file SiPixelDigisCUDA.cc.

References cms::cuda::assert().

    : m_store(cms::cuda::make_device_unique<SiPixelDigisCUDA::StoreType[]>(
          SiPixelDigisCUDASOAView::roundFor128ByteAlignment(maxFedWords) *
              static_cast<int>(SiPixelDigisCUDASOAView::StorageLocation::kMAX),
          stream)),
      m_view(m_store, maxFedWords, SiPixelDigisCUDASOAView::StorageLocation::kMAX) {
  assert(maxFedWords != 0);
}

~SiPixelDigisCUDA()

SiPixelDigisCUDA::~SiPixelDigisCUDA ( )

default

SiPixelDigisCUDA() [3/4]

SiPixelDigisCUDA::SiPixelDigisCUDA ( const SiPixelDigisCUDA &  )

delete

SiPixelDigisCUDA() [4/4]

SiPixelDigisCUDA::SiPixelDigisCUDA ( SiPixelDigisCUDA &&  )

default

Member Function Documentation

copyAllToHostAsync()

cms::cuda::host::unique_ptr< SiPixelDigisCUDA::StoreType[]> SiPixelDigisCUDA::copyAllToHostAsync

(

cudaStream_t

stream

)

const

Definition at line 17 of file SiPixelDigisCUDA.cc.

References SiPixelDigisCUDASOAView::clus(), cudaCheck, SiPixelDigisCUDASOAView::kMAX, m_view, nDigis(), runTheMatrix::ret, SiPixelDigisCUDASOAView::roundFor128ByteAlignment(), and cms::cuda::stream.

                               {
  auto ret = cms::cuda::make_host_unique<StoreType[]>(
      m_view.roundFor128ByteAlignment(nDigis()) * static_cast<int>(SiPixelDigisCUDASOAView::StorageLocationHost::kMAX),
      stream);
  cudaCheck(cudaMemcpyAsync(ret.get(),
                            m_view.clus(),
                            m_view.roundFor128ByteAlignment(nDigis()) * sizeof(SiPixelDigisCUDA::StoreType) *
                                static_cast<int>(SiPixelDigisCUDASOAView::StorageLocationHost::kMAX),
                            cudaMemcpyDeviceToHost,
                            stream));
  return ret;
}

nDigis()

uint32_t SiPixelDigisCUDA::nDigis ( ) const

inline

Definition at line 29 of file SiPixelDigisCUDA.h.

References nDigis_h.

Referenced by copyAllToHostAsync(), and setNModulesDigis().

{ return nDigis_h; }

nModules()

uint32_t SiPixelDigisCUDA::nModules ( ) const

inline

Definition at line 28 of file SiPixelDigisCUDA.h.

References nModules_h.

Referenced by setNModulesDigis().

{ return nModules_h; }

operator=() [1/2]

SiPixelDigisCUDA& SiPixelDigisCUDA::operator= ( const SiPixelDigisCUDA &  )

delete

operator=() [2/2]

SiPixelDigisCUDA& SiPixelDigisCUDA::operator= ( SiPixelDigisCUDA &&  )

default

setNModulesDigis()

void SiPixelDigisCUDA::setNModulesDigis ( uint32_t  nModules, uint32_t  nDigis  )

inline

Definition at line 23 of file SiPixelDigisCUDA.h.

References nDigis(), nDigis_h, nModules(), and nModules_h.

Referenced by pixelgpudetails::SiPixelRawToClusterGPUKernel::getResults().

                                                            {
    nModules_h = nModules;
    nDigis_h = nDigis;
  }

view() [1/2]

SiPixelDigisCUDASOAView SiPixelDigisCUDA::view ( )

inline

Definition at line 33 of file SiPixelDigisCUDA.h.

References m_view.

{ return m_view; }

view() [2/2]

SiPixelDigisCUDASOAView const SiPixelDigisCUDA::view ( ) const

inline

Definition at line 34 of file SiPixelDigisCUDA.h.

References m_view.

{ return m_view; }

Member Data Documentation

m_store

cms::cuda::device::unique_ptr<StoreType[]> SiPixelDigisCUDA::m_store

private

Definition at line 38 of file SiPixelDigisCUDA.h.

m_view

SiPixelDigisCUDASOAView SiPixelDigisCUDA::m_view

private

Definition at line 40 of file SiPixelDigisCUDA.h.

Referenced by copyAllToHostAsync(), and view().

nDigis_h

uint32_t SiPixelDigisCUDA::nDigis_h = 0

private

Definition at line 43 of file SiPixelDigisCUDA.h.

Referenced by nDigis(), and setNModulesDigis().

nModules_h

uint32_t SiPixelDigisCUDA::nModules_h = 0

private

Definition at line 42 of file SiPixelDigisCUDA.h.

Referenced by nModules(), and setNModulesDigis().