1

我对 OpenCL 内核内部寄存器的使用有点困惑。我正在使用 -cl-nv-verbose 来捕获内核的寄存器使用情况。目前，我的内核正在记录内核中ptxas info: Used 4 registers的一些代码。对于以下部分：

double a;
a = pow(2.0,2.0)
if (index != 0) {
}

使用的寄存器发生了变化ptxas info: Used 6 registers。我知道 if 循环中没有任何内容。但是，如果我再次重组为：

double a;
if (index != 0) {
    a = pow(2.0,2.0)
}

这会将寄存器用法更改为ptxas info: Used 15 registers. 我不会更改内核的工作组大小。也许答案在于查看 ptx 代码，但我不明白（尽管如果需要我可以得到它）。我更感兴趣的是，为什么只移动一行代码，寄存器使用量就跳到了两倍。有任何想法吗？（指数为private）

更新：PTX 代码之前和之后

更新：内核代码：

__kernel void butterfC( __global double *sI,    
                        __global double *sJ,
                        __global double *sK,
                        const int zR, 
                        const int yR,   
                        const int xR,
                        unsigned int l1,
                        const int dir,
                        unsigned int type   ) 
{
    int idX = get_global_id(0);
    int idY = get_global_id(1);
    int idZ = get_global_id(2);

    int BASE = idZ*xR*yR;
    int STRIDE = 1;

    int powX = pow(4.0f,l1);
    int powXm1 = pow(4.0f,l1-1);

    int yIndex, kIndex;

    switch(type)
    {
        case 1: BASE += idY*xR; 
                yIndex  = idX / powXm1 * powX;
                kIndex  = (idX % powXm1) + yIndex;  
                break;
        case 2: BASE += idX; STRIDE = xR; 
                yIndex  = idY / powXm1 * powX;
                kIndex  = idY % powXm1 + yIndex;
                break;
        case 3: BASE = idY*xR + idX; STRIDE = xR * yR; 
                yIndex  = idZ / powXm1 * powX;
                kIndex  = idZ % powXm1 + yIndex;
                break; 
    }

    double a;   

    //a = pow(2.0,2.0);
    if (kIndex != 0) {
        a = pow(2.0,2.0);
        .... do stuff
    }
}
4

0 回答 0