hcal::raw::ElectronicsMappingGPU Class Reference

#include <ElectronicsMappingGPU.h>

Classes
struct	Product

Public Member Functions
	ElectronicsMappingGPU (HcalElectronicsMap const &)
Product const &	getProduct (cudaStream_t) const
	~ElectronicsMappingGPU ()=default

Private Attributes
std::vector< uint32_t, cms::cuda::HostAllocator< uint32_t > >	eid2did_
std::vector< uint32_t, cms::cuda::HostAllocator< uint32_t > >	eid2tid_
cms::cuda::ESProduct< Product >	product_

Detailed Description

Definition at line 14 of file ElectronicsMappingGPU.h.

Constructor & Destructor Documentation

ElectronicsMappingGPU()

hcal::raw::ElectronicsMappingGPU::ElectronicsMappingGPU

(

HcalElectronicsMap const &

mapping

)

Definition at line 12 of file ElectronicsMappingGPU.cc.

References runTauDisplay::eid, eid2did_, eid2tid_, mps_fire::i, and HPSPFTaus_cff::mapping.

        : eid2tid_(HcalElectronicsId::maxLinearIndex, 0u), eid2did_(HcalElectronicsId::maxLinearIndex, 0u) {
      auto const& eidsPrecision = mapping.allElectronicsIdPrecision();
      for (uint32_t i = 0; i < eidsPrecision.size(); ++i) {
        auto const& eid = eidsPrecision[i];

        // assign
        eid2did_[eid.linearIndex()] = eid.isTriggerChainId() ? 0u : mapping.lookup(eid).rawId();
      }

      auto const& eidsTrigger = mapping.allElectronicsIdTrigger();
      for (uint32_t i = 0; i < eidsTrigger.size(); i++) {
        auto const& eid = eidsTrigger[i];

        // assign
        eid2tid_[eid.linearIndex()] = eid.isTriggerChainId() ? mapping.lookupTrigger(eid).rawId() : 0u;
      }
    }

~ElectronicsMappingGPU()

hcal::raw::ElectronicsMappingGPU::~ElectronicsMappingGPU ( )

default

Member Function Documentation

getProduct()

ElectronicsMappingGPU::Product const & hcal::raw::ElectronicsMappingGPU::getProduct

(

cudaStream_t

cudaStream

)

const

Definition at line 37 of file ElectronicsMappingGPU.cc.

References cudaCheck, hcal::raw::ElectronicsMappingGPU::Product::eid2did, eid2did_, hcal::raw::ElectronicsMappingGPU::Product::eid2tid, eid2tid_, and product_.

                                                                                                       {
      auto const& product = product_.dataForCurrentDeviceAsync(
          cudaStream, [this](ElectronicsMappingGPU::Product& product, cudaStream_t cudaStream) {
            // malloc
            cudaCheck(cudaMalloc((void**)&product.eid2did, this->eid2did_.size() * sizeof(uint32_t)));
            cudaCheck(cudaMalloc((void**)&product.eid2tid, this->eid2tid_.size() * sizeof(uint32_t)));

            // transfer
            cudaCheck(cudaMemcpyAsync(product.eid2did,
                                      this->eid2did_.data(),
                                      this->eid2did_.size() * sizeof(uint32_t),
                                      cudaMemcpyHostToDevice,
                                      cudaStream));
            cudaCheck(cudaMemcpyAsync(product.eid2tid,
                                      this->eid2tid_.data(),
                                      this->eid2tid_.size() * sizeof(uint32_t),
                                      cudaMemcpyHostToDevice,
                                      cudaStream));
          });

      return product;
    }

Member Data Documentation

eid2did_

std::vector<uint32_t, cms::cuda::HostAllocator<uint32_t> > hcal::raw::ElectronicsMappingGPU::eid2did_

private

Definition at line 39 of file ElectronicsMappingGPU.h.

Referenced by ElectronicsMappingGPU(), and getProduct().

eid2tid_

std::vector<uint32_t, cms::cuda::HostAllocator<uint32_t> > hcal::raw::ElectronicsMappingGPU::eid2tid_

private

Definition at line 38 of file ElectronicsMappingGPU.h.

Referenced by ElectronicsMappingGPU(), and getProduct().

product_

cms::cuda::ESProduct<Product> hcal::raw::ElectronicsMappingGPU::product_

private

Definition at line 41 of file ElectronicsMappingGPU.h.

Referenced by getProduct().