2012-04-04 78 views
6

我是OpenCL的初学者,我试图让下面的内核工作。当我运行该程序时,在内核程序的构建过程中出现错误。更具体的错误如下:OpenCL结构参数无效的地址空间

Error: Failed to build program executable! 
<program source>:19:64: error: invalid address space for argument to __kernel function 
__kernel void accelarate_flow(__global const   t_param params, 
                  ^

你可以在这里看到内核。一开始我认为这是因为我没有在内核中定义的结构,但即使添加它们,问题依然存在。我在这里做错了什么?

const char *accelerate_flow_kernel_source = 
#pragma OPENCL EXTENSION cl_khr_fp64 : enable         
typedef struct                 
{                    
    int nx;                 
    int ny;                 
    int maxIters;                
    int reynolds_dim;               
    double density;                
    double accel;                
    double omega;                
} t_param;                  

typedef struct                 
{                    
    double speeds[9];               
} t_speed;                  

__kernel void accelarate_flow(__global const   t_param params,   
           __global const   int*  obstacles,  
           __global    t_speed* cells,   
             const unsigned int  count)   
{                    
    int pos = get_global_id(0);             
    if(pos >= count || pos % params.nx != 0) return;        
    double w1,w2;                
    w1 = params.density * params.accel/9.0;         
    w2 = params.density * params.accel/36.0;         
    if(!obstacles[pos] &&              
    (cells[pos].speeds[3] - w1) > 0.0 &&          
    (cells[pos].speeds[6] - w2) > 0.0 &&          
    (cells[pos].speeds[7] - w2) > 0.0)          
    {                   
    cells[pos].speeds[1] += w1;            
    cells[pos].speeds[5] += w2;            
    cells[pos].speeds[8] += w2;            
    cells[pos].speeds[3] -= w1;            
    cells[pos].speeds[6] -= w2;            
    cells[pos].speeds[7] -= w2;            
    }                   
}                    

回答

4

global是一个指针预选赛(地址空间),所以你必须通过global const t_param* params

+0

谢谢。这确实是个问题。我在看到您的回复之前正在测试它,并回过头来评论我找到了解决方案。 – gkaran89 2012-04-04 20:35:22

+0

我发现它一般很好(不知道这种情况),看看来自不同编译器(例如AMD,Intel)的错误;并非所有这些都对所有情况都有帮助。 – eudoxos 2012-04-04 20:37:17