@@ -687,8 +687,7 @@ void SDL::Event::addPixelSegmentToEvent(std::vector<unsigned int> hitIndices0,st
687687 cudaStreamSynchronize (stream);
688688 nTotalMDs+= N_MAX_PIXEL_MD_PER_MODULES;
689689 cudaFree (device_nTotalMDs);
690- createMDsInExplicitMemory (*mdsInGPU, nTotalMDs, nLowerModules, N_MAX_PIXEL_MD_PER_MODULES,stream);
691-
690+ createMDsInExplicitMemory (*mdsInGPU, nTotalMDs, nLowerModules, N_MAX_PIXEL_MD_PER_MODULES,stream);
692691 cudaMemcpyAsync (mdsInGPU->nMemoryLocations , &nTotalMDs, sizeof (unsigned int ), cudaMemcpyHostToDevice, stream);
693692 cudaStreamSynchronize (stream);
694693
@@ -902,14 +901,14 @@ void SDL::Event::createMiniDoublets()
902901{
903902 // hardcoded range numbers for this will come from studies!
904903 unsigned int nTotalMDs;
905- unsigned int *device_nTotalMDs;
906- cudaMalloc ((void **)&device_nTotalMDs, sizeof (unsigned int ));
907- cudaMemsetAsync (&rangesInGPU->miniDoubletModuleOccupancy [nLowerModules],N_MAX_PIXEL_MD_PER_MODULES, sizeof (unsigned int ),stream);
908- createMDArrayRangesGPU<<<1 ,1024 ,0 ,stream>>> (*modulesInGPU, *rangesInGPU, device_nTotalMDs);
909- cudaMemcpyAsync (&nTotalMDs,device_nTotalMDs,sizeof (unsigned int ),cudaMemcpyDeviceToHost,stream);
910- cudaStreamSynchronize (stream);
911- nTotalMDs+=N_MAX_PIXEL_MD_PER_MODULES;
912- cudaFree (device_nTotalMDs);
904+ unsigned int *device_nTotalMDs;
905+ cudaMalloc ((void **)&device_nTotalMDs, sizeof (unsigned int ));
906+ cudaMemsetAsync (&rangesInGPU->miniDoubletModuleOccupancy [nLowerModules],N_MAX_PIXEL_MD_PER_MODULES, sizeof (unsigned int ),stream);
907+ createMDArrayRangesGPU<<<1 ,1024 ,0 ,stream>>> (*modulesInGPU, *rangesInGPU, device_nTotalMDs);
908+ cudaMemcpyAsync (&nTotalMDs,device_nTotalMDs,sizeof (unsigned int ),cudaMemcpyDeviceToHost,stream);
909+ cudaStreamSynchronize (stream);
910+ nTotalMDs+=N_MAX_PIXEL_MD_PER_MODULES;
911+ cudaFree (device_nTotalMDs);
913912
914913 if (mdsInGPU == nullptr )
915914 {
0 commit comments