<html xmlns:v="urn:schemas-microsoft-com:vml" xmlns:o="urn:schemas-microsoft-com:office:office" xmlns:w="urn:schemas-microsoft-com:office:word" xmlns:m="http://schemas.microsoft.com/office/2004/12/omml" xmlns="http://www.w3.org/TR/REC-html40"> <head> <meta http-equiv="Content-Type" content="text/html; charset=us-ascii"> <meta name="Generator" content="Microsoft Word 14 (filtered medium)"> <style></style> </head> <body lang="EN-US" link="blue" vlink="purple"> <div class="WordSection1"> I am not sure if this is the appropriate list on which to ask this question, if not hopefully someone can suggest an alternative.<o:p></o:p> <o:p> </o:p> Under Linux, I am attempting to perform an offline compile of an OpenCL kernel example using Clang, and then load that binary using the clCreateProgramWithBinary() function.<o:p></o:p> <o:p> </o:p> Unfortunately, while clover is loading the binary, I end up getting a segmentation fault:<o:p></o:p> <o:p> </o:p> Program received signal SIGSEGV, Segmentation fault.<o:p></o:p> proc (v=..., is=...) at core/module.cpp:50<o:p></o:p> 50 T x;<o:p></o:p> <o:p> </o:p> I have pasted the source code I am using below, for both the kernel and the host code.<o:p></o:p> <o:p> </o:p> I am compiling with the following commands:<o:p></o:p> clang -target r600-unknown-unknown -x cl -S -emit-llvm -mcpu=r600 kernel.cl -o kernel.clbin <o:p></o:p> clang -g -L/usr/local/lib -lOpenCL offline_host.c -o offline_host<o:p></o:p> <o:p> </o:p> I have LLVM/Clang 3.4RC3 installed and Mesa 10.0.1.<o:p></o:p> <o:p> </o:p> If anyone has suggestions, or can point me to the appropriate mailing list or documentation, I’d appreciate it.<o:p></o:p> <o:p> </o:p> Thanks!<o:p></o:p> -Al<o:p></o:p> <o:p> </o:p> <o:p> </o:p> Source code for “kernel.cl”<o:p></o:p> ====================<o:p></o:p> __kernel void vecAdd(__global float* a)<o:p></o:p> {<o:p></o:p> int gid = get_global_id(0);<o:p></o:p> a[gid] += a[gid];<o:p></o:p> }<o:p></o:p> <o:p> </o:p> <o:p> </o:p> Source code for “offline_host.c”<o:p></o:p> ==========================<o:p></o:p> #include <stdio.h><o:p></o:p> #include <stdlib.h><o:p></o:p> <o:p> </o:p> #ifdef __APPLE__<o:p></o:p> #include <OpenCL/opencl.h><o:p></o:p> #else<o:p></o:p> #include <CL/cl.h><o:p></o:p> #endif<o:p></o:p> <o:p> </o:p> #define MEM_SIZE (128)<o:p></o:p> #define MAX_BINARY_SIZE (0x100000)<o:p></o:p> <o:p> </o:p> int main()<o:p></o:p> {<o:p></o:p> cl_platform_id platform_id = NULL;<o:p></o:p> cl_device_id device_id = NULL;<o:p></o:p> cl_context context = NULL;<o:p></o:p> cl_command_queue command_queue = NULL;<o:p></o:p> cl_mem memobj = NULL;<o:p></o:p> cl_program program = NULL;<o:p></o:p> cl_kernel kernel = NULL;<o:p></o:p> cl_uint ret_num_devices;<o:p></o:p> cl_uint ret_num_platforms;<o:p></o:p> cl_int ret;<o:p></o:p> <o:p> </o:p> float mem[MEM_SIZE];<o:p></o:p> <o:p> </o:p> FILE *fp;<o:p></o:p> char fileName[] = "kernel.clbin";<o:p></o:p> size_t binary_size;<o:p></o:p> char *binary_buf;<o:p></o:p> cl_int binary_status;<o:p></o:p> cl_int i;<o:p></o:p> <o:p> </o:p> /* Load kernel binary */<o:p></o:p> fp = fopen(fileName, "r");<o:p></o:p> if (!fp) {<o:p></o:p> fprintf(stderr, “Failed to load kernel.\n”);<o:p></o:p> exit(1);<o:p></o:p> }<o:p></o:p> binary_buf = (char *)malloc(MAX_BINARY_SIZE);<o:p></o:p> binary_size = fread(binary_buf, 1, MAX_BINARY_SIZE, fp);<o:p></o:p> fclose(fp);<o:p></o:p> <o:p> </o:p> /* Initialize input data */<o:p></o:p> for (i = 0; i < MEM_SIZE; i++) {<o:p></o:p> mem[i] = i;<o:p></o:p> }<o:p></o:p> <o:p> </o:p> /* Get platform/device information */<o:p></o:p> ret = clGetPlatformIDs(1, &platform_id, &ret_num_platforms);<o:p></o:p> ret = clGetDeviceIDs(platform_id, CL_DEVICE_TYPE_GPU, 1, &device_id, &ret_num_devices);<o:p></o:p> <o:p> </o:p> /* Create OpenCL context*/<o:p></o:p> context = clCreateContext(NULL, 1, &device_id, NULL, NULL, &ret);<o:p></o:p> <o:p> </o:p> /* Create command queue */<o:p></o:p> command_queue = clCreateCommandQueue(context, device_id, 0, &ret);<o:p></o:p> <o:p> </o:p> /* Create memory buffer */<o:p></o:p> memobj = clCreateBuffer(context, CL_MEM_READ_WRITE, MEM_SIZE * sizeof(float), NULL, &ret);<o:p></o:p> <o:p> </o:p> /* Transfer data over to the memory buffer */<o:p></o:p> ret = clEnqueueWriteBuffer(command_queue, memobj, CL_TRUE, 0, MEM_SIZE * sizeof(float), mem, 0, NULL, NULL);<o:p></o:p> <o:p> </o:p> /* Create kernel program from the kernel binary */<o:p></o:p> program = clCreateProgramWithBinary(context, 1, &device_id, (const size_t *)&binary_size,<o:p></o:p> (const unsigned char **)&binary_buf, &binary_status, &ret);<o:p></o:p> <o:p> </o:p> /* Create OpenCL kernel */<o:p></o:p> kernel = clCreateKernel(program, "vecAdd", &ret);<o:p></o:p> printf("err:%d\n", ret);<o:p></o:p> <o:p> </o:p> /* Set OpenCL kernel arguments */<o:p></o:p> ret = clSetKernelArg(kernel, 0, sizeof(cl_mem), (void *)&memobj);<o:p></o:p> <o:p> </o:p> size_t global_work_size[3] = {MEM_SIZE, 0, 0};<o:p></o:p> size_t local_work_size[3] = {MEM_SIZE, 0, 0};<o:p></o:p> <o:p> </o:p> /* Execute OpenCL kernel */<o:p></o:p> ret = clEnqueueNDRangeKernel(command_queue, kernel, 1, NULL, global_work_size, local_work_size, 0, NULL, NULL);<o:p></o:p> <o:p> </o:p> /* Copy result from the memory buffer */<o:p></o:p> ret = clEnqueueReadBuffer(command_queue, memobj, CL_TRUE, 0, MEM_SIZE * sizeof(float), mem, 0, NULL, NULL);<o:p></o:p> <o:p> </o:p> /* Display results */<o:p></o:p> for (i=0; i < MEM_SIZE; i++) {<o:p></o:p> printf(“mem[%d] : $f\n”, i, mem[i]);<o:p></o:p> }<o:p></o:p> <o:p> </o:p> /* Finalization */<o:p></o:p> ret = clFlush(command_queue);<o:p></o:p> ret = clFinish(command_queue);<o:p></o:p> ret = clReleaseKernel(kernel);<o:p></o:p> ret = clReleaseProgram(program);<o:p></o:p> ret = clReleaseMemObject(memobj);<o:p></o:p> ret = clReleaseCommandQueue(command_queue);<o:p></o:p> ret = clReleaseContext(context);<o:p></o:p> <o:p> </o:p> free(binary_buf);<o:p></o:p> <o:p> </o:p> return 0;<o:p></o:p> }<o:p></o:p> <o:p> </o:p> <o:p> </o:p> Al Dorrington<o:p></o:p> Software Engineer Sr<o:p></o:p> Lockheed Martin, Mission Systems and Training<o:p></o:p> <a href="mailto:albert.dorrington@lmco.com">albert.dorrington@lmco.com</a> / 607-751-4859<o:p></o:p> <o:p> </o:p> </div> </body> </html>