SiStripClustersCUDAHost Class Reference

#include <SiStripClustersCUDA.h>

Inheritance diagram for SiStripClustersCUDAHost:

Public Member Functions
SiStripClustersCUDAHost &	operator= (const SiStripClustersCUDAHost &)=delete
SiStripClustersCUDAHost &	operator= (SiStripClustersCUDAHost &&)=default
	SiStripClustersCUDAHost ()=default
	SiStripClustersCUDAHost (const SiStripClustersCUDADevice &clusters_d, cudaStream_t stream)
	SiStripClustersCUDAHost (const SiStripClustersCUDAHost &)=delete
	SiStripClustersCUDAHost (SiStripClustersCUDAHost &&)=default
	~SiStripClustersCUDAHost () override=default
Public Member Functions inherited from SiStripClustersSOABase< cms::cuda::host::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

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

Detailed Description

Definition at line 47 of file SiStripClustersCUDA.h.

Constructor & Destructor Documentation

SiStripClustersCUDAHost() [1/4]

SiStripClustersCUDAHost::SiStripClustersCUDAHost ( )

default

SiStripClustersCUDAHost() [2/4]

SiStripClustersCUDAHost::SiStripClustersCUDAHost ( const SiStripClustersCUDADevice &  clusters_d, cudaStream_t  stream  )

explicit

Definition at line 36 of file SiStripClustersCUDA.cc.

References SiStripClustersSOABase< T >::barycenter(), SiStripClustersSOABase< cms::cuda::host::unique_ptr >::barycenter_, SiStripClustersSOABase< T >::charge(), SiStripClustersSOABase< cms::cuda::host::unique_ptr >::charge_, SiStripClustersSOABase< T >::clusterADCs(), SiStripClustersSOABase< cms::cuda::host::unique_ptr >::clusterADCs_, SiStripClustersSOABase< T >::clusterDetId(), SiStripClustersSOABase< cms::cuda::host::unique_ptr >::clusterDetId_, SiStripClustersSOABase< T >::clusterIndex(), SiStripClustersSOABase< cms::cuda::host::unique_ptr >::clusterIndex_, SiStripClustersSOABase< T >::clusterSize(), SiStripClustersSOABase< cms::cuda::host::unique_ptr >::clusterSize_, cms::cuda::copyAsync(), cudaCheck, SiStripClustersSOABase< T >::firstStrip(), SiStripClustersSOABase< cms::cuda::host::unique_ptr >::firstStrip_, SiStripClustersCUDADevice::maxClusterSize(), SiStripClustersSOABase< cms::cuda::host::unique_ptr >::maxClusterSize_, SiStripClustersCUDADevice::nClusters(), SiStripClustersSOABase< cms::cuda::host::unique_ptr >::nClusters_, cms::cuda::stream, SiStripClustersSOABase< T >::trueCluster(), and SiStripClustersSOABase< cms::cuda::host::unique_ptr >::trueCluster_.

                                                                                                                 {
  nClusters_ = clusters_d.nClusters();
  maxClusterSize_ = clusters_d.maxClusterSize();
  clusterIndex_ = cms::cuda::make_host_unique<uint32_t[]>(nClusters_, stream);
  clusterSize_ = cms::cuda::make_host_unique<uint32_t[]>(nClusters_, stream);
  clusterADCs_ = cms::cuda::make_host_unique<uint8_t[]>(nClusters_ * maxClusterSize_, stream);
  clusterDetId_ = cms::cuda::make_host_unique<stripgpu::detId_t[]>(nClusters_, stream);
  firstStrip_ = cms::cuda::make_host_unique<stripgpu::stripId_t[]>(nClusters_, stream);
  trueCluster_ = cms::cuda::make_host_unique<bool[]>(nClusters_, stream);
  barycenter_ = cms::cuda::make_host_unique<float[]>(nClusters_, stream);
  charge_ = cms::cuda::make_host_unique<float[]>(nClusters_, stream);

  cms::cuda::copyAsync(clusterIndex_, clusters_d.clusterIndex(), nClusters_, stream);
  cms::cuda::copyAsync(clusterSize_, clusters_d.clusterSize(), nClusters_, stream);
  cms::cuda::copyAsync(clusterADCs_, clusters_d.clusterADCs(), nClusters_ * maxClusterSize_, stream);
  cms::cuda::copyAsync(clusterDetId_, clusters_d.clusterDetId(), nClusters_, stream);
  cms::cuda::copyAsync(firstStrip_, clusters_d.firstStrip(), nClusters_, stream);
  cms::cuda::copyAsync(trueCluster_, clusters_d.trueCluster(), nClusters_, stream);
  cms::cuda::copyAsync(barycenter_, clusters_d.barycenter(), nClusters_, stream);
  cms::cuda::copyAsync(charge_, clusters_d.charge(), nClusters_, stream);
#ifdef GPU_CHECK
  cudaCheck(cudaStreamSynchronize(stream));
#endif
}

~SiStripClustersCUDAHost()

SiStripClustersCUDAHost::~SiStripClustersCUDAHost ( )

overridedefault

SiStripClustersCUDAHost() [3/4]

SiStripClustersCUDAHost::SiStripClustersCUDAHost ( const SiStripClustersCUDAHost &  )

delete

SiStripClustersCUDAHost() [4/4]

SiStripClustersCUDAHost::SiStripClustersCUDAHost ( SiStripClustersCUDAHost &&  )

default

Member Function Documentation

operator=() [1/2]

SiStripClustersCUDAHost& SiStripClustersCUDAHost::operator= ( const SiStripClustersCUDAHost &  )

delete

operator=() [2/2]

SiStripClustersCUDAHost& SiStripClustersCUDAHost::operator= ( SiStripClustersCUDAHost &&  )

default