Skip to content

Commit 2cf3b47

Browse files
committed
Fix compiler warnings
1 parent 0457082 commit 2cf3b47

File tree

2 files changed

+4
-4
lines changed

2 files changed

+4
-4
lines changed

GPU/GPUTracking/DataCompression/GPUTPCDecompressionKernels.cxx

+3-3
Original file line numberDiff line numberDiff line change
@@ -30,7 +30,7 @@ GPUdii() void GPUTPCDecompressionKernels::Thread<GPUTPCDecompressionKernels::ste
3030

3131
const unsigned int maxTime = (param.par.continuousMaxTimeBin + 1) * ClusterNative::scaleTimePacked - 1;
3232

33-
for (unsigned int i = trackStart + get_global_id(0); i < trackEnd; i += get_global_size(0)) {
33+
for (int i = trackStart + get_global_id(0); i < trackEnd; i += get_global_size(0)) {
3434
decompressTrack(cmprClusters, param, maxTime, i, decompressor.mAttachedClustersOffsets[i], decompressor);
3535
}
3636
}
@@ -133,10 +133,10 @@ GPUdii() void GPUTPCDecompressionKernels::Thread<GPUTPCDecompressionKernels::ste
133133
ClusterNative* GPUrestrict() clusterBuffer = decompressor.mNativeClustersBuffer;
134134
const ClusterNativeAccess* outputAccess = processors.ioPtrs.clustersNative;
135135
unsigned int* offsets = decompressor.mUnattachedClustersOffsets;
136-
for (unsigned int i = get_global_id(0); i < GPUCA_ROW_COUNT * nSlices; i += get_global_size(0)) {
136+
for (int i = get_global_id(0); i < GPUCA_ROW_COUNT * nSlices; i += get_global_size(0)) {
137137
unsigned int iRow = i % GPUCA_ROW_COUNT;
138138
unsigned int iSlice = sliceStart + (i / GPUCA_ROW_COUNT);
139-
const int linearIndex = iSlice * GPUCA_ROW_COUNT + iRow;
139+
const unsigned int linearIndex = iSlice * GPUCA_ROW_COUNT + iRow;
140140
unsigned int tmpBufferIndex = computeLinearTmpBufferIndex(iSlice, iRow, decompressor.mMaxNativeClustersPerBuffer);
141141
ClusterNative* buffer = clusterBuffer + outputAccess->clusterOffset[iSlice][iRow];
142142
if (decompressor.mNativeClustersIndex[linearIndex] != 0) {

GPU/GPUTracking/Global/GPUChainTrackingCompression.cxx

+1-1
Original file line numberDiff line numberDiff line change
@@ -286,7 +286,7 @@ int GPUChainTracking::RunTPCDecompression()
286286
runKernel<GPUMemClean16>({GetGridAutoStep(inputStream, RecoStep::TPCDecompression), krnlRunRangeNone, &mEvents->init}, DecompressorShadow.mNativeClustersIndex, NSLICES * GPUCA_ROW_COUNT * sizeof(DecompressorShadow.mNativeClustersIndex[0]));
287287
std::exclusive_scan(cmprClsHost.nTrackClusters, cmprClsHost.nTrackClusters + cmprClsHost.nTracks, Decompressor.mAttachedClustersOffsets, 0u); // computing clusters offsets for first kernel
288288
int nStreams = doGPU ? mRec->NStreams() - 1 : 1;
289-
for (unsigned int iStream = 0; iStream < nStreams; ++iStream) {
289+
for (int iStream = 0; iStream < nStreams; ++iStream) {
290290
unsigned int startTrack = cmprClsHost.nTracks / nStreams * iStream;
291291
unsigned int endTrack = cmprClsHost.nTracks / nStreams * (iStream + 1) + (iStream < nStreams - 1 ? 0 : cmprClsHost.nTracks % nStreams); // index of last track (excluded from computation)
292292
unsigned int numTracks = endTrack - startTrack;

0 commit comments

Comments
 (0)