我必须将此代码从 c ++ 并行化到 CUDA C
for(ihist = 0; ihist < numhist; ihist++){
for(iwin = 0; iwin<numwin; iwin++){
denwham[ihist] += (numbinwin[iwin]/g[iwin])*exp(F[iwin]-U[ihist]);
}
Punnorm[ihist] = numwham[ihist]/denwham[ihist];
}
在 CUDA C 中,使用 sum reduction :
extern __shared__ float sdata[];
int tx = threadIdx.x;
int i=blockIdx.x;
int j=blockIdx.y;
float sum=0.0;
float temp=0.0;
temp=U[j];
if(tx<numwin)
{
sum=(numbinwin[tx]/g[tx])*exp(F[tx]- temp);
sdata[tx] = sum;
__syncthreads();
}
for(int offset = blockDim.x / 2;offset > 0;offset >>= 1)
{
if(tx < offset)
{
// add a partial sum upstream to our own
sdata[tx] += sdata[tx + offset];
}
__syncthreads();
}
// finally, thread 0 writes the result
if(threadIdx.x == 0)
{
// note that the result is per-block
// not per-thread
denwham[i] = sdata[0];
for(int k=0;k<numhist;k++)
Punnorm[k] = numwham[k]/denwham[k];
}
并以这种方式初始化它:
int smem_sz = (256)*sizeof(float);
dim3 Block(numhist,numhist,1);
NewProbabilitiesKernel<<<Block,256,smem_sz>>>(...);
我的问题是我无法使用 U 迭代exp
,我尝试了以下方法:
a) loop for/while inside the kernel that iterates over U
b) iterate by thread
c) iterate to block
所有这些尝试都导致我在 C++ 代码和代码 cuda 之间得出不同的结果。如果我放置一个常量而不是 U [i],则代码可以正常工作!
你有什么想法可以帮助我吗?
谢谢。