Skip to content

Commit 3c55949

Browse files
authored
ITS: GPU add needed synchronization (#14439)
1 parent ead329b commit 3c55949

File tree

1 file changed

+4
-0
lines changed

1 file changed

+4
-0
lines changed

Detectors/ITSMFT/ITS/tracking/GPU/cuda/TrackingKernels.cu

Lines changed: 4 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -1217,6 +1217,8 @@ void processNeighboursHandler(const int startLayer,
12171217
maxChi2ClusterAttachment,
12181218
propagator,
12191219
matCorrType);
1220+
GPUChkErrS(cudaPeekAtLastError());
1221+
GPUChkErrS(cudaDeviceSynchronize());
12201222
12211223
int level = startLevel;
12221224
thrust::device_vector<int, gpu::TypedAllocator<int>> lastCellId(allocInt);
@@ -1276,6 +1278,8 @@ void processNeighboursHandler(const int startLayer,
12761278
maxChi2ClusterAttachment,
12771279
propagator,
12781280
matCorrType);
1281+
GPUChkErrS(cudaPeekAtLastError());
1282+
GPUChkErrS(cudaDeviceSynchronize());
12791283
}
12801284
thrust::device_vector<CellSeed, gpu::TypedAllocator<CellSeed>> outSeeds(updatedCellSeed.size(), allocCellSeed);
12811285
auto end = thrust::copy_if(updatedCellSeed.begin(), updatedCellSeed.end(), outSeeds.begin(), gpu::seed_selector(1.e3, maxChi2NDF * ((startLevel + 2) * 2 - 5)));

0 commit comments

Comments
 (0)