Variadic Macros in OpenCL: Where are they supported? -


i have been trying find information on (non-standard, cf. 1.0, 1.1, 1.2, 2.0) support variadic macros in opencl implementations.

i have access following platforms, of support variadic macros:

  • mac os x, intel cpu, opencl 1.2, driver: 1.1
  • mac os x, intel gpu, opencl 1.2, driver: 1.2(dec 23 2014 00:18:31)
  • mac os x, ati gpu, opencl 1.2, driver: 1.2 (aug 17 2014 20:27:52)
  • mac os x, nvidia gpu, opencl 1.2, driver: 10.2.7 310.41.25f01

could other please check available implementations can have map of implementations supported variadic macros?

edit: here self-contained test program makes uses of variadic macro.

#include <stdlib.h> #include <stdio.h>  #ifdef __apple__ #include <opencl/opencl.h> #else #include <cl/cl.h> #endif  const char* source = "#define kernel(name, ...) kernel void name(__va_args__) \n" "                                                        \n" "kernel(test, global float* input, global float* output) \n" "{                                                       \n" "    int = get_global_id(0);                           \n" "    output[i] = input[i];                               \n" "}                                                       \n" "                                                        \n" ;  static const int gpu = 1;  int main(int argc, char** argv) {     int err;      cl_float input[16];     cl_float output[16];      size_t global = 16;     size_t local = 16;      cl_platform_id platform_id;     cl_device_id device_id;     cl_context context;     cl_command_queue command_queue;     cl_program program;     cl_kernel kernel;     cl_mem input_buf;     cl_mem output_buf;      err = clgetplatformids(1, &platform_id, null);     if(err != cl_success)     {         printf("error: clgetplatformids\n");         return exit_failure;     }      err = clgetdeviceids(platform_id, gpu ? cl_device_type_gpu : cl_device_type_cpu, 1, &device_id, null);     if(err != cl_success)     {         printf("error: clgetdeviceids\n");         return exit_failure;     }      context = clcreatecontext(0, 1, &device_id, null, null, &err);     if(err != cl_success)     {         printf("error: clcreatecontext\n");         return exit_failure;     }      command_queue = clcreatecommandqueue(context, device_id, 0, &err);     if(err != cl_success)     {         printf("error: clcreatecommandqueue\n");         return exit_failure;     }      program = clcreateprogramwithsource(context, 1, &source, null, &err);     if(err != cl_success)     {         printf("error: clcreateprogramwithsource\n");         return exit_failure;     }      err = clbuildprogram(program, 0, null, null, null, null);     if (err != cl_success)     {         size_t len;         char buffer[2048];          printf("error: clbuildprogram\n");         clgetprogrambuildinfo(program, device_id, cl_program_build_log, sizeof(buffer), buffer, &len);         printf("%s\n", buffer);          return exit_failure;     }      kernel = clcreatekernel(program, "test", &err);     if(err != cl_success)     {         printf("error: clcreatekernel\n");         return exit_failure;     }      input_buf = clcreatebuffer(context, cl_mem_read_only, 16*sizeof(cl_float), null, null);     output_buf = clcreatebuffer(context, cl_mem_write_only, 16*sizeof(cl_float), null, null);     if(!input_buf || !output_buf)     {         printf("error: clcreatebuffer\n");         return exit_failure;     }      err = clenqueuewritebuffer(command_queue, input_buf, cl_true, 0, 16*sizeof(cl_float), input, 0, null, null);     if(err != cl_success)     {         printf("error: clenqueuewritebuffer\n");         return exit_failure;     }      err = 0;     err |= clsetkernelarg(kernel, 0, sizeof(cl_mem), &input_buf);     err |= clsetkernelarg(kernel, 1, sizeof(cl_mem), &output_buf);     if(err != cl_success)     {         printf("error: clsetkernelarg\n");         return exit_failure;     }      err = clenqueuendrangekernel(command_queue, kernel, 1, null, &global, &local, 0, null, null);     if(err != cl_success)     {         printf("error: clenqueuendrangekernel\n");         return exit_failure;     }      clfinish(command_queue);      err = clenqueuereadbuffer(command_queue, output_buf, cl_true, 0, 16*sizeof(cl_float), output, 0, null, null );     if(err != cl_success)     {         printf("error: clenqueuereadbuffer\n");         return exit_failure;     }      clreleasememobject(input_buf);     clreleasememobject(output_buf);     clreleaseprogram(program);     clreleasekernel(kernel);     clreleasecommandqueue(command_queue);     clreleasecontext(context);      printf("success\n");      return exit_success; }

for posterity, answer myself list of platforms tested support of variadic macros. future visitor, please feel free add platform can test list.

supported:

  • mac os x, intel cpu, opencl 1.2, driver: 1.1
  • mac os x, intel gpu, opencl 1.2, driver: 1.2(dec 23 2014 00:18:31)
  • mac os x, ati gpu, opencl 1.2, driver: 1.2 (aug 17 2014 20:27:52)
  • debian unstable, amd gpu, opencl 2.0, driver: amdgpu-pro 16.15.2-277429
  • mac os x, nvidia gpu, opencl 1.2, driver: 10.2.7 310.41.25f01
  • redhat enterprise linux 5, nvidia cuda sdk 4.0, opencl 1.0 cuda, driver: 260.19.26

unsupported:

  • debian unstable, intel gpu, opencl 1.2, driver: beignet 1.1.1

Comments

Post a Comment

Popular posts from this blog

c++ - Difference between pre and post decrement in recursive function argument -

i have following sample code used pre-decrement void function(int c) { if(c == 0) { return; } else { cout << "dp" << c << endl; function(--c); cout << c << endl; return; } } this function give output input 4 : dp3 dp2 dp1 dp0 0 1 2 3 but when use post decrement void function(int c) { if(c == 0) { return; } else { cout << "dp" << c << endl; function(c--); cout << c << endl; return; } } output goes in infinite loop dp4 can explain me in detail why happens ? this happens because function(c--) called same value of c , when finishes c decremented. recursively called, hence called same value no chance of return , hit stack overflow error. assume this, int x = 1, y = 0; y = x++ result y == 1 , x == 2. if y = ++x , bot x , y 2.
Read more

php - Nothing but 'run(); ' when browsing to my local project, how do I fix this? -

i added new project. made mistake in projectname.conf file in sites-available apache2, led me reinstalling apache2. after reinstalling , re-enabling projects on every page of every project .. <body> run(); </body> .. i've run composer update, restarted service, restarted pc, checked config files, tried disabling new project. there nothing in error log, , access.log: 127.0.0.1 - - [15/may/2015:01:40:47 +0200] "get / http/1.1" 304 181 "-" "mozilla/5.0 (x11; ubuntu; linux x86_64; rv:38.0) gecko/20100101 firefox/38.0" maybe i'm forgetting apache2 reinstall? don't think did different last time installed it. looks haven't setup php correctly. take @ this great guide , maybe you're forgetting link php config apache2.
Read more

php - How can I echo out this array? -

i don't know how go grabbing data in variable , put foreach loop. class tree{ private $info = array( array('name'=>'jim','state'=>'nu','company'=>'nu','phone'=>array('cell'=>'5615111111','office'=>'5611111111'),'email'=>array('primary'=>'exs@example.com','ex@there.com')), array('name'=>'joe smith','city'=>'phoenix','phone'=>'4805551111','email'=>'jsmith@some_email.com'), array('name'=>'john doe','city'=>'chandler','company'=>'doe co.','email'=>array('jdoe@gmail.com','personal'=>'email@email.com'),'phone'=>'6025550002') ); } if you're inside of class, can access private variable using $this->variablename . example, i...
Read more