Opencl kernel build error 11

I am using ATI RV770 graphics card, OpenCl 1.0 and ati-stream-sdk-v2.3-lnx64 on linux.

While running my host code which includes following two sections to build kernel program, i am getting error code (-11) i.e. cl_build_program_failure. Does it means that kernel program compiled, if not then how is it compiled and debugged?

const char* KernelPath = "abc_kernel.cl";   //kernel program is in separate file but in same directory of host code..

/* Create Program object from the kernel source *******/

char* sProgramSource = readKernelSource(KernelPath);
size_t sourceSize =  strlen(sProgramSource) ;
program = clCreateProgramWithSource(context, 1,(const char **) &sProgramSource,&sourceSize, &err);
checkStatus("error while creating program",err);

/* Build (compile & Link ) Program *******/

char* options = (char* )malloc(10*sizeof(char));
strcpy(options, "-g");
err = clBuildProgram(program, num_devices, devices_id, options, NULL, NULL);
checkStatus("Build Program Failed", err); //This line throwing the error....

function to read kernel program is as follows::

/* read program source file*/

char* readKernelSource(const char* kernelSourcePath){
 FILE    *fp = NULL;
 size_t  sourceLength;
 char    *sourceString ;
 fp = fopen( kernelSourcePath , "r");
 if(fp == 0)
 {
        printf("failed to open file");
        return NULL;
 }
 // get the length of the source code
 fseek(fp, 0, SEEK_END);
 sourceLength = ftell(fp);
 rewind(fp);
 // allocate a buffer for the source code string and read it in
 sourceString = (char *)malloc( sourceLength + 1);
 if( fread( sourceString, 1, sourceLength, fp) !=sourceLength )
 {
          printf("nt Error : Fail to read file ");
          return 0;
 }
 sourceString[sourceLength+1]='';
 fclose(fp);
 return sourceString;

}// end of readKernelSource

Can anyone tell how to fix it?

Does it means that it is OpenCl compilation error at runtime or something else?

//Printing build_log info using clGetProgramBuildInfo() as below, But why is is not printing anything?

char* build_log;
size_t log_size;

// First call to know the proper size
        err = clGetProgramBuildInfo(program, devices_id, CL_PROGRAM_BUILD_LOG, 0, NULL, &log_size);
        build_log = (char* )malloc((log_size+1));

        // Second call to get the log
        err = clGetProgramBuildInfo(program, devices_id, CL_PROGRAM_BUILD_LOG, log_size, build_log, NULL);
        build_log[log_size] = '';
        printf("--- Build log ---n ");
        fprintf(stderr, "%sn", build_log);
        free(build_log);

Describe the bug
ethminer fails to run on systems with amdgpu/mesa drivers

To Reproduce
Steps to reproduce the behavior:

1. Download and extract binary from github releases
2. ./bin/ethminer -G -M 123

Expected behavior
ethminer succesfully starts up, runs test and prints hashrate.

Screenshots (Optional)

$ ./bin/ethminer -G -M 123

ethminer 0.19.0-alpha.0
Build: linux/release/gnu

i 10:28:43 ethminer Selected pool localhost:0
i 10:28:43 ethminer Established connection to localhost:0
i 10:28:43 ethminer Spinning up miners…
cl 10:28:43 cl-0 OpenCL OpenCL 1.1 Mesa 20.3.4 not supported, but platform Clover might work nevertheless. USE AT OWN RISK!
cl 10:28:43 cl-0 Using PciId : AMD VEGAM (DRM 3.40.0, 5.10.12-200.fc33.x86_64, LLVM 11.0.0) OpenCL 1.1 Mesa 20.3.4 Memory : 4.00 GB
i 10:28:43 sim Epoch : 0 Difficulty : 4.29 Gh
i 10:28:43 sim Job: bcb4e018… block 123 localhost:0
cl 10:28:43 cl-0 Generating DAG + Light : 1.02 GB
cl 10:28:43 cl-0 OpenCL kernel
X 10:28:43 cl-0 OpenCL kernel build log:
input.cl:321:9: error: implicit declaration of function ‘amd_bitalign’ is invalid in OpenCL
input.cl:180:9: note: expanded from macro ‘KECCAK_PROCESS’
input.cl:99:60: note: expanded from macro ‘KECCAKF_1600_RND’
input.cl:87:24: note: expanded from macro ‘ROTL64_1’
input.cl:433:5: error: implicit declaration of function ‘amd_bitalign’ is invalid in OpenCL
input.cl:180:9: note: expanded from macro ‘KECCAK_PROCESS’
input.cl:99:60: note: expanded from macro ‘KECCAKF_1600_RND’
input.cl:87:24: note: expanded from macro ‘ROTL64_1’

X 10:28:43 cl-0 OpenCL kernel build error (-11):
clBuildProgram
SIGSEGV encountered …
stack trace:
backtrace() returned 7 addresses
./bin/ethminer() [0x426929]
/lib64/libc.so.6(+0x3da60) [0x7f99f10a3a60]
./bin/ethminer() [0x6e3ca3]
./bin/ethminer() [0x4bbdef]
./bin/ethminer() [0x7bdb20]
/lib64/libpthread.so.0(+0x93f9) [0x7f99f139b3f9]
/lib64/libc.so.6(clone+0x43) [0x7f99f1167b53]

Environment (please complete the following information):

• Operating System: Fedora 33, linux v5.10.12rpm , mesa v20.3.4
• Hardware: Radeon RX Vega M GL
• Ethminer Version [0.16, 0.17, 0.18, 0.19-alpha0]
• Ethminer options used: -G -M 123

Additional context
ethmoner v0.15 works succesfully. It starts failing with v0.16

Я использую видеокарту ATI RV770, OpenCl 1.0 и ati-stream-sdk-v2.3-lnx64 в Linux.

При запуске моего хост-кода, который включает следующие два раздела для создания программы ядра, я получаю код ошибки (-11), т.е. cl_build_program_failure. Означает ли это, что программа ядра скомпилирована, если нет, то как она компилируется и отлаживается?

const char* KernelPath = "abc_kernel.cl";   //kernel program is in separate file but in same directory of host code..

/* Создать объект Program из исходного кода ядра *******/

char* sProgramSource = readKernelSource(KernelPath);
size_t sourceSize =  strlen(sProgramSource) ;
program = clCreateProgramWithSource(context, 1,(const char **) &sProgramSource,&sourceSize, &err);
checkStatus("error while creating program",err);

/* Построить (скомпилировать и связать) программу **** /

char* options = (char* )malloc(10*sizeof(char));
strcpy(options, "-g");
err = clBuildProgram(program, num_devices, devices_id, options, NULL, NULL);
checkStatus("Build Program Failed", err); //This line throwing the error....

Функция чтения программы ядра выглядит следующим образом:

/ * читать исходный файл программы * /

char* readKernelSource(const char* kernelSourcePath){
 FILE    *fp = NULL;
 size_t  sourceLength;
 char    *sourceString ;
 fp = fopen( kernelSourcePath , "r");
 if(fp == 0)
 {
        printf("failed to open file");
        return NULL;
 }
 // get the length of the source code
 fseek(fp, 0, SEEK_END);
 sourceLength = ftell(fp);
 rewind(fp);
 // allocate a buffer for the source code string and read it in
 sourceString = (char *)malloc( sourceLength + 1);
 if( fread( sourceString, 1, sourceLength, fp) !=sourceLength )
 {
          printf("nt Error : Fail to read file ");
          return 0;
 }
 sourceString[sourceLength+1]='';
 fclose(fp);
 return sourceString;

} // конец readKernelSource

Может кто подскажет как исправить?

Означает ли это, что это ошибка компиляции OpenCl во время выполнения или что-то еще?

// Печать информации build_log с помощью clGetProgramBuildInfo (), как показано ниже, но почему он ничего не печатает?

char * build_log; size_t log_size;

// First call to know the proper size
        err = clGetProgramBuildInfo(program, devices_id, CL_PROGRAM_BUILD_LOG, 0, NULL, &log_size);
        build_log = (char* )malloc((log_size+1));

        // Second call to get the log
        err = clGetProgramBuildInfo(program, devices_id, CL_PROGRAM_BUILD_LOG, log_size, build_log, NULL);
        build_log[log_size] = '';
        printf("--- Build log ---n ");
        fprintf(stderr, "%sn", build_log);
        free(build_log);

Вопрос:

cl_program program;
program = clCreateProgramWithSource(context, 1, (const char**) &kernel_string, NULL, &err);
if(err != CL_SUCCESS)
{
cout<<"Unable to create Program Object. Error code = "<<err<<endl;
exit(1);
}
if(clBuildProgram(program, 0, NULL, NULL, NULL, NULL) != CL_SUCCESS)
{
cout<<"Program Build failedn";
size_t length;
char buffer[2048];
clGetProgramBuildInfo(program, device_id[0], CL_PROGRAM_BUILD_LOG, sizeof(buffer), buffer, &length);
cout<<"--- Build log ---n "<<buffer<<endl;
exit(1);
}

Ответ №1

Ответ №2

err = clBuildProgram(program, 0, NULL, NULL, NULL, NULL);

////////////////Add the following lines to see the log file///////////

if (err != CL_SUCCESS) {
char *buff_erro;
cl_int errcode;
size_t build_log_len;
errcode = clGetProgramBuildInfo(program, devices[0], CL_PROGRAM_BUILD_LOG, 0, NULL, &build_log_len);
if (errcode) {
printf("clGetProgramBuildInfo failed at line %dn", __LINE__);
exit(-1);
}

buff_erro = malloc(build_log_len);
if (!buff_erro) {
printf("malloc failed at line %dn", __LINE__);
exit(-2);
}

errcode = clGetProgramBuildInfo(program, devices[0], CL_PROGRAM_BUILD_LOG, build_log_len, buff_erro, NULL);
if (errcode) {
printf("clGetProgramBuildInfo failed at line %dn", __LINE__);
exit(-3);
}

fprintf(stderr,"Build log: n%sn", buff_erro); //Be careful with  the fprint
free(buff_erro);
fprintf(stderr,"clBuildProgram failedn");
exit(EXIT_FAILURE);
}

Ответ №3

Я столкнулся с той же проблемой с пустым файлом журнала. Я тестировал свое ядро ​​ocl на другом компьютере. У него было 2 платформы вместо одного. Один графический процессор Intel и один графический процессор AMD. У меня только был установлен SDK AMD OCL. Проблема с установкой Intel OCL SDK. Также исправлен выбор платформы AMD вместо платформы Intel GPU.

checkerror(clBuildProgram(program, deviceidcount, deviceids.data(), nullptr, nullptr, nullptr));

__kernel void render(double playerx,double playery,double playerz,double yaw,double pitch,double x1,double y1,double z1,double x2,double y2,double z2,double x3,double y3,double z3,__global int* texture){
//const int i = get_global_id(0);
//x[i] = a*x[i];
//x[i] = cos(a);
x1 = x1-playerx;
y1 = y1-playery;
z1 = z1-playerz;
x2 = x2-playerx;
y2 = y2-playery;
z2 = z2-playerz;
x3 = x3-playerx;
y3 = y3-playery;
z3 = z3-playerz;

double smallyaw = yaw - M_PI_2;
double bigpitch = pitch + M_PI_2;

double screenx1 = cos(smallyaw)*cos(pitch)*x1 + sin(smallyaw)*cos(pitch)*y1 + sin(pitch)*z1;
double screeny1 = cos(yaw)*cos(bigpitch)*x1 + sin(yaw)*cos(bigpitch)*y1 + sin(bigpitch)*z1;
double screenz1 = cos(yaw)*cos(pitch)*x1 + sin(yaw)*cos(pitch)*y1 + sin(pitch)*z1;
printf(screenx1);
printf(screeny1);
printf(screenz1);
}

Решение

printf("value = %#gn", 3.012);

Другие решения

if i == 0{
printf(...)
}

printf("%f", value);

I have the following AMD graphics card and I have been trying to use it for GPU accelerated computing using OpenCL mesa driver. I am trying to use ArrayFire for the computation and after posting a couple of issues about it in the ArrayFire github page, found that the issue is with the Mesa driver for Arch.

0d:00.0 Display controller: Advanced Micro Devices, Inc. [AMD/ATI] Sun XT [Radeon HD 8670A/8670M/8690M / R5 M330 / M430 / Radeon 520 Mobile] (rev 83)
	Subsystem: Hewlett-Packard Company Device 80c2
	Flags: bus master, fast devsel, latency 0, IRQ 52
	Memory at b0000000 (64-bit, prefetchable) [size=256M]
	Memory at d4000000 (64-bit, non-prefetchable) [size=256K]
	I/O ports at 4000 [size=256]
	Expansion ROM at d4040000 [disabled] [size=128K]
	Capabilities: <access denied>
	Kernel driver in use: radeon
	Kernel modules: radeon, amdgpu

I tried using the mesa driver with OpenCl support in the official repositories, but found that it is buggy and would always result in some error. Also, it does not support any higher version other than OpenCL 1.1. After a distro hop to Ubuntu, I used the mesa driver from Oibaf’s PPA and it seemed to work pretty well. After some searching, I found that an equivalent in Arch is the mesa-git driver. Now, in my Arch, I installed the compiled mesa-git and opencl-mesa-git from Laurent Carlier’s repository. After, testing it with Julia I find the following errors.

julia> a = AFArray(rand(4,4))
AFArray: 4×4 Array{Float64,2}:
 0.910863  0.528568   0.769485  0.262519
 0.758505  0.59156    0.464172  0.498584
 0.888846  0.839448   0.482488  0.179536
 0.470455  0.0313732  0.784979  0.995334

julia> a+1
AFArray: Error showing value of type AFArray{Float64,2}:
ERROR: ArrayFire Error (998) : Internal error
OpenCL Error (-11): Build Program Failure when calling clBuildProgram
Stacktrace:
 [1] _error(::UInt32, ::Bool) at /home/<username>/.julia/packages/ArrayFire/wYxcd/src/util.jl:96
 [2] _error at /home/<username>/.julia/packages/ArrayFire/wYxcd/src/util.jl:85 [inlined]
 [3] get_data_ptr at /home/<username>/.julia/packages/ArrayFire/wYxcd/src/wrap.jl:748 [inlined]
 [4] convert_array(::AFArray{Float64,2}) at /home/<username>/.julia/packages/ArrayFire/wYxcd/src/util.jl:216
 [5] Array at /home/<username>/.julia/packages/ArrayFire/wYxcd/src/array.jl:33 [inlined]
 [6] toa(::AFArray{Float64,2}) at /home/<username>/.julia/packages/ArrayFire/wYxcd/src/util.jl:48
 [7] show(::IOContext{REPL.Terminals.TTYTerminal}, ::MIME{Symbol("text/plain")}, ::AFArray{Float64,2}) at /home/<username>/.julia/packages/ArrayFire/wYxcd/src/util.jl:52
 [8] display(::REPL.REPLDisplay, ::MIME{Symbol("text/plain")}, ::Any) at /build/julia/src/julia-1.4.2/usr/share/julia/stdlib/v1.4/REPL/src/REPL.jl:137
 [9] display(::REPL.REPLDisplay, ::Any) at /build/julia/src/julia-1.4.2/usr/share/julia/stdlib/v1.4/REPL/src/REPL.jl:141
 [10] display(::Any) at ./multimedia.jl:323
 [11] #invokelatest#1 at ./essentials.jl:712 [inlined]
 [12] invokelatest at ./essentials.jl:711 [inlined]
 [13] print_response(::IO, ::Any, ::Bool, ::Bool, ::Any) at /build/julia/src/julia-1.4.2/usr/share/julia/stdlib/v1.4/REPL/src/REPL.jl:161
 [14] print_response(::REPL.AbstractREPL, ::Any, ::Bool, ::Bool) at /build/julia/src/julia-1.4.2/usr/share/julia/stdlib/v1.4/REPL/src/REPL.jl:146
 [15] (::REPL.var"#do_respond#38"{Bool,REPL.var"#48#57"{REPL.LineEditREPL,REPL.REPLHistoryProvider},REPL.LineEditREPL,REPL.LineEdit.Prompt})(::Any, ::Any, ::Any) at /build/julia/src/julia-1.4.2/usr/share/julia/stdlib/v1.4/REPL/src/REPL.jl:729

So, it seems the mesa-git is also buggy in my case. My question is why are the drivers on Mesa buggy and can it be fixed? Also, is there any way that I can install the drivers from Oibaf’s PPA(which are for Ubuntu) on Arch as they seem to work without any errors? You help here would be great as I will then be able to do my calculations without the need to switch over from Arch.

Linux <username> 5.7.3-arch1-1 #1 SMP PREEMPT Wed, 17 Jun 2020 19:42:12 +0000 x86_64 GNU/Linux

Further information: I am using the latest Arch kernel and have just updated all my drivers after a fresh reinstall a couple of days ago. I would be happy to provide any other information as needed. Thank you

Last edited by Lattitude (2020-06-21 04:23:29)