SiStripClustersCUDADevice Class Reference

#include <SiStripClustersCUDA.h>

Inheritance diagram for SiStripClustersCUDADevice:

Classes
struct	DeviceView

Public Member Functions
uint32_t	maxClusterSize () const
uint32_t *	maxClusterSizePtr ()
uint32_t	nClusters () const
uint32_t *	nClustersPtr ()
SiStripClustersCUDADevice &	operator= (const SiStripClustersCUDADevice &)=delete
SiStripClustersCUDADevice &	operator= (SiStripClustersCUDADevice &&)=default
	SiStripClustersCUDADevice ()=default
	SiStripClustersCUDADevice (uint32_t maxClusters, uint32_t maxStripsPerCluster, cudaStream_t stream)
	SiStripClustersCUDADevice (const SiStripClustersCUDADevice &)=delete
	SiStripClustersCUDADevice (SiStripClustersCUDADevice &&)=default
DeviceView *	view () const
	~SiStripClustersCUDADevice () override=default
Public Member Functions inherited from SiStripClustersSOABase< cms::cuda::device::unique_ptr >
const auto &	barycenter () const
auto &	barycenter ()
const auto &	charge () const
auto &	charge ()
const auto &	clusterADCs () const
auto &	clusterADCs ()
const auto &	clusterDetId () const
auto &	clusterDetId ()
const auto &	clusterIndex () const
auto &	clusterIndex ()
const auto &	clusterSize () const
auto &	clusterSize ()
const auto &	firstStrip () const
auto &	firstStrip ()
uint32_t	maxClusterSize () const
uint32_t	nClusters () const
SiStripClustersSOABase &	operator= (const SiStripClustersSOABase &)=delete
SiStripClustersSOABase &	operator= (SiStripClustersSOABase &&)=default
void	setMaxClusterSize (uint32_t maxClusterSize)
void	setNClusters (uint32_t nClusters)
	SiStripClustersSOABase ()=default
	SiStripClustersSOABase (const SiStripClustersSOABase &)=delete
	SiStripClustersSOABase (SiStripClustersSOABase &&)=default
const auto &	trueCluster () const
auto &	trueCluster ()
virtual	~SiStripClustersSOABase ()=default

Private Attributes
uint32_t	maxClusterSize_
uint32_t	nClusters_
cms::cuda::device::unique_ptr< DeviceView >	view_d

Additional Inherited Members
Protected Attributes inherited from SiStripClustersSOABase< cms::cuda::device::unique_ptr >
cms::cuda::device::unique_ptr< float[]>	barycenter_
cms::cuda::device::unique_ptr< float[]>	charge_
cms::cuda::device::unique_ptr< uint8_t[]>	clusterADCs_
cms::cuda::device::unique_ptr< stripgpu::detId_t[]>	clusterDetId_
cms::cuda::device::unique_ptr< uint32_t[]>	clusterIndex_
cms::cuda::device::unique_ptr< uint32_t[]>	clusterSize_
cms::cuda::device::unique_ptr< stripgpu::stripId_t[]>	firstStrip_
uint32_t	maxClusterSize_
uint32_t	nClusters_
cms::cuda::device::unique_ptr< bool[]>	trueCluster_

Detailed Description

Definition at line 11 of file SiStripClustersCUDA.h.

Constructor & Destructor Documentation

SiStripClustersCUDADevice() [1/4]

SiStripClustersCUDADevice::SiStripClustersCUDADevice ( )

default

SiStripClustersCUDADevice() [2/4]

SiStripClustersCUDADevice::SiStripClustersCUDADevice ( uint32_t  maxClusters, uint32_t  maxStripsPerCluster, cudaStream_t  stream  )

explicit

Definition at line 4 of file SiStripClustersCUDA.cc.

References SiStripClustersCUDADevice::DeviceView::barycenter_, SiStripClustersSOABase< cms::cuda::device::unique_ptr >::barycenter_, SiStripClustersCUDADevice::DeviceView::charge_, SiStripClustersSOABase< cms::cuda::device::unique_ptr >::charge_, SiStripClustersCUDADevice::DeviceView::clusterADCs_, SiStripClustersSOABase< cms::cuda::device::unique_ptr >::clusterADCs_, SiStripClustersCUDADevice::DeviceView::clusterDetId_, SiStripClustersSOABase< cms::cuda::device::unique_ptr >::clusterDetId_, SiStripClustersCUDADevice::DeviceView::clusterIndex_, SiStripClustersSOABase< cms::cuda::device::unique_ptr >::clusterIndex_, SiStripClustersCUDADevice::DeviceView::clusterSize_, SiStripClustersSOABase< cms::cuda::device::unique_ptr >::clusterSize_, cms::cuda::copyAsync(), cudaCheck, SiStripClustersCUDADevice::DeviceView::firstStrip_, SiStripClustersSOABase< cms::cuda::device::unique_ptr >::firstStrip_, ALCARECOSiStripCalZeroBias_cff::maxClusters, SiStripClustersCUDADevice::DeviceView::maxClusterSize_, maxClusterSize_, cms::cuda::stream, SiStripClustersCUDADevice::DeviceView::trueCluster_, SiStripClustersSOABase< cms::cuda::device::unique_ptr >::trueCluster_, view(), and view_d.

                                                                          {
  maxClusterSize_ = maxStripsPerCluster;

  clusterIndex_ = cms::cuda::make_device_unique<uint32_t[]>(maxClusters, stream);
  clusterSize_ = cms::cuda::make_device_unique<uint32_t[]>(maxClusters, stream);
  clusterADCs_ = cms::cuda::make_device_unique<uint8_t[]>(maxClusters * maxStripsPerCluster, stream);
  clusterDetId_ = cms::cuda::make_device_unique<stripgpu::detId_t[]>(maxClusters, stream);
  firstStrip_ = cms::cuda::make_device_unique<stripgpu::stripId_t[]>(maxClusters, stream);
  trueCluster_ = cms::cuda::make_device_unique<bool[]>(maxClusters, stream);
  barycenter_ = cms::cuda::make_device_unique<float[]>(maxClusters, stream);
  charge_ = cms::cuda::make_device_unique<float[]>(maxClusters, stream);

  auto view = cms::cuda::make_host_unique<DeviceView>(stream);
  view->clusterIndex_ = clusterIndex_.get();
  view->clusterSize_ = clusterSize_.get();
  view->clusterADCs_ = clusterADCs_.get();
  view->clusterDetId_ = clusterDetId_.get();
  view->firstStrip_ = firstStrip_.get();
  view->trueCluster_ = trueCluster_.get();
  view->barycenter_ = barycenter_.get();
  view->charge_ = charge_.get();
  view->maxClusterSize_ = maxStripsPerCluster;

  view_d = cms::cuda::make_device_unique<DeviceView>(stream);
  cms::cuda::copyAsync(view_d, view, stream);
#ifdef GPU_CHECK
  cudaCheck(cudaStreamSynchronize(stream));
#endif
}

~SiStripClustersCUDADevice()

SiStripClustersCUDADevice::~SiStripClustersCUDADevice ( )

overridedefault

SiStripClustersCUDADevice() [3/4]

SiStripClustersCUDADevice::SiStripClustersCUDADevice ( const SiStripClustersCUDADevice &  )

delete

SiStripClustersCUDADevice() [4/4]

SiStripClustersCUDADevice::SiStripClustersCUDADevice ( SiStripClustersCUDADevice &&  )

default

Member Function Documentation

maxClusterSize()

uint32_t SiStripClustersCUDADevice::maxClusterSize ( ) const

inline

Definition at line 38 of file SiStripClustersCUDA.h.

References maxClusterSize_.

Referenced by SiStripClustersCUDAHost::SiStripClustersCUDAHost().

{ return maxClusterSize_; }

maxClusterSizePtr()

uint32_t* SiStripClustersCUDADevice::maxClusterSizePtr ( )

inline

Definition at line 39 of file SiStripClustersCUDA.h.

References maxClusterSize_.

{ return &maxClusterSize_; }

nClusters()

uint32_t SiStripClustersCUDADevice::nClusters ( ) const

inline

Definition at line 36 of file SiStripClustersCUDA.h.

References nClusters_.

Referenced by SiStripClustersCUDAHost::SiStripClustersCUDAHost().

{ return nClusters_; }

nClustersPtr()

uint32_t* SiStripClustersCUDADevice::nClustersPtr ( )

inline

Definition at line 37 of file SiStripClustersCUDA.h.

References nClusters_.

{ return &nClusters_; }

operator=() [1/2]

SiStripClustersCUDADevice& SiStripClustersCUDADevice::operator= ( const SiStripClustersCUDADevice &  )

delete

operator=() [2/2]

SiStripClustersCUDADevice& SiStripClustersCUDADevice::operator= ( SiStripClustersCUDADevice &&  )

default

view()

DeviceView* SiStripClustersCUDADevice::view ( ) const

inline

Definition at line 35 of file SiStripClustersCUDA.h.

References view_d.

Referenced by SiStripClustersCUDADevice().

{ return view_d.get(); }

Member Data Documentation

maxClusterSize_

uint32_t SiStripClustersCUDADevice::maxClusterSize_

private

Definition at line 44 of file SiStripClustersCUDA.h.

Referenced by maxClusterSize(), maxClusterSizePtr(), and SiStripClustersCUDADevice().

nClusters_

uint32_t SiStripClustersCUDADevice::nClusters_

private

Definition at line 43 of file SiStripClustersCUDA.h.

Referenced by nClusters(), and nClustersPtr().

view_d

cms::cuda::device::unique_ptr<DeviceView> SiStripClustersCUDADevice::view_d

private

Definition at line 42 of file SiStripClustersCUDA.h.

Referenced by SiStripClustersCUDADevice(), and view().