#include <ElectronicsMappingGPU.h>

Classes
struct	Product

Public Member Functions
	ElectronicsMappingGPU (HcalElectronicsMap const &)

const Product &	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.

         : 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;
       }
     }

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

◆ ~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.

                                                                                                        {
       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;
     }