ViewVC Help
View File | Revision Log | Show Annotations | Download File
/cvs/OpenCL/OpenCL.pm
(Generate patch)

Comparing OpenCL/OpenCL.pm (file contents):
Revision 1.23 by root, Sun Nov 20 22:29:36 2011 UTC vs.
Revision 1.49 by root, Sat Apr 21 20:48:03 2012 UTC

… …
101 101
102Best run this once to get a feel for the platforms and devices in your 102Best run this once to get a feel for the platforms and devices in your
103system. 103system.
104 104
105 for my $platform (OpenCL::platforms) { 105 for my $platform (OpenCL::platforms) {
106 printf "platform: %s\n", $platform->info (OpenCL::PLATFORM_NAME); 106 printf "platform: %s\n", $platform->name;
107 printf "extensions: %s\n", $platform->info (OpenCL::PLATFORM_EXTENSIONS); 107 printf "extensions: %s\n", $platform->extensions;
108 for my $device ($platform->devices) { 108 for my $device ($platform->devices) {
109 printf "+ device: %s\n", $device->info (OpenCL::DEVICE_NAME); 109 printf "+ device: %s\n", $device->name;
110 my $ctx = $device->context; 110 my $ctx = $platform->context (undef, [$device]);
111 # do stuff 111 # do stuff
112 } 112 }
113 } 113 }
114 114
115=head2 Get a useful context and a command queue. 115=head2 Get a useful context and a command queue.
… …
149 149
150=head2 Create and build a program, then create a kernel out of one of its 150=head2 Create and build a program, then create a kernel out of one of its
151functions. 151functions.
152 152
153 my $src = ' 153 my $src = '
154 __kernel void 154 kernel void
155 squareit (__global float *input, __global float *output) 155 squareit (global float *input, global float *output)
156 { 156 {
157 $id = get_global_id (0); 157 $id = get_global_id (0);
158 output [id] = input [id] * input [id]; 158 output [id] = input [id] * input [id];
159 } 159 }
160 '; 160 ';
161 161
162 my $prog = $ctx->program_with_source ($src); 162 my $prog = $ctx->program_with_source ($src);
163 163
164 # build croaks on compile errors, so catch it and print the compile errors 164 # build croaks on compile errors, so catch it and print the compile errors
165 eval { $prog->build ($dev); 1 } 165 eval { $prog->build ($dev, "-cl-fast-relaxed-math"); 1 }
166 or die $prog->build_info ($dev, OpenCL::PROGRAM_BUILD_LOG); 166 or die $prog->build_log;
167 167
168 my $kernel = $prog->kernel ("squareit"); 168 my $kernel = $prog->kernel ("squareit");
169 169
170=head2 Create some input and output float buffers, then call the 170=head2 Create some input and output float buffers, then call the
171'squareit' kernel on them. 171'squareit' kernel on them.
… …
210 # enqueue an async read 210 # enqueue an async read
211 $ev = $queue->enqueue_read_buffer ($output, 0, 0, OpenCL::SIZEOF_FLOAT * 4, my $data, $ev); 211 $ev = $queue->enqueue_read_buffer ($output, 0, 0, OpenCL::SIZEOF_FLOAT * 4, my $data, $ev);
212 212
213 # wait for the last event to complete 213 # wait for the last event to complete
214 $ev->wait; 214 $ev->wait;
215
216=head2 Use the OpenGL module to share a texture between OpenCL and OpenGL and draw some julia
217set tunnel effect.
218
219This is quite a long example to get you going.
220
221 use OpenGL ":all";
222 use OpenCL;
223
224 # open a window and create a gl texture
225 OpenGL::glpOpenWindow width => 256, height => 256;
226 my $texid = glGenTextures_p 1;
227 glBindTexture GL_TEXTURE_2D, $texid;
228 glTexImage2D_c GL_TEXTURE_2D, 0, GL_RGBA8, 256, 256, 0, GL_RGBA, GL_UNSIGNED_BYTE, 0;
229
230 # find and use the first opencl device that let's us get a shared opengl context
231 my $platform;
232 my $dev;
233 my $ctx;
234
235 for (OpenCL::platforms) {
236 $platform = $_;
237 for ($platform->devices) {
238 $dev = $_;
239 $ctx = $platform->context ([OpenCL::GLX_DISPLAY_KHR, undef, OpenCL::GL_CONTEXT_KHR, undef], [$dev])
240 and last;
241 }
242 }
243
244 $ctx
245 or die "cannot find suitable OpenCL device\n";
246
247 my $queue = $ctx->queue ($dev);
248
249 # now attach an opencl image2d object to the opengl texture
250 my $tex = $ctx->gl_texture2d (OpenCL::MEM_WRITE_ONLY, GL_TEXTURE_2D, 0, $texid);
251
252 # now the boring opencl code
253 my $src = <<EOF;
254 kernel void
255 juliatunnel (write_only image2d_t img, float time)
256 {
257 float2 p = (float2)(get_global_id (0), get_global_id (1)) / 256.f * 2.f - 1.f;
258
259 float2 m = (float2)(1.f, p.y) / fabs (p.x);
260 m.x = fabs (fmod (m.x + time * 0.05f, 4.f)) - 2.f;
261
262 float2 z = m;
263 float2 c = (float2)(sin (time * 0.05005), cos (time * 0.06001));
264
265 for (int i = 0; i < 25 && dot (z, z) < 4.f; ++i)
266 z = (float2)(z.x * z.x - z.y * z.y, 2.f * z.x * z.y) + c;
267
268 float3 colour = (float3)(z.x, z.y, z.x * z.y);
269 write_imagef (img, (int2)(get_global_id (0), get_global_id (1)), (float4)(colour * p.x * p.x, 1.));
270 }
271 EOF
272 my $prog = $ctx->program_with_source ($src);
273 eval { $prog->build ($dev); 1 }
274 or die $prog->build_log ($dev);
275
276 my $kernel = $prog->kernel ("juliatunnel");
277
278 # program compiled, kernel ready, now draw and loop
279
280 for (my $time; ; ++$time) {
281 # acquire objects from opengl
282 $queue->enqueue_acquire_gl_objects ([$tex]);
283
284 # configure and run our kernel
285 $kernel->set_image2d (0, $tex);
286 $kernel->set_float (1, $time);
287 $queue->enqueue_nd_range_kernel ($kernel, undef, [256, 256], undef);
288
289 # release objects to opengl again
290 $queue->enqueue_release_gl_objects ([$tex]);
291
292 # wait
293 $queue->finish;
294
295 # now draw the texture, the defaults should be all right
296 glTexParameterf GL_TEXTURE_2D, GL_TEXTURE_MIN_FILTER, GL_NEAREST;
297
298 glEnable GL_TEXTURE_2D;
299 glBegin GL_QUADS;
300 glTexCoord2f 0, 1; glVertex3i -1, -1, -1;
301 glTexCoord2f 0, 0; glVertex3i 1, -1, -1;
302 glTexCoord2f 1, 0; glVertex3i 1, 1, -1;
303 glTexCoord2f 1, 1; glVertex3i -1, 1, -1;
304 glEnd;
305
306 glXSwapBuffers;
307
308 select undef, undef, undef, 1/60;
309 }
215 310
216=head1 DOCUMENTATION 311=head1 DOCUMENTATION
217 312
218=head2 BASIC CONVENTIONS 313=head2 BASIC CONVENTIONS
219 314
… …
241=item * Structures are often specified by flattening out their components 336=item * Structures are often specified by flattening out their components
242as with short vectors, and returned as arrayrefs. 337as with short vectors, and returned as arrayrefs.
243 338
244=item * When enqueuing commands, the wait list is specified by adding 339=item * When enqueuing commands, the wait list is specified by adding
245extra arguments to the function - anywhere a C<$wait_events...> argument 340extra arguments to the function - anywhere a C<$wait_events...> argument
246is documented this can be any number of event objects. 341is documented this can be any number of event objects. As an extsnion
342implemented by this module, C<undef> values will be ignored in the event
343list.
247 344
248=item * When enqueuing commands, if the enqueue method is called in void 345=item * When enqueuing commands, if the enqueue method is called in void
249context, no event is created. In all other contexts an event is returned 346context, no event is created. In all other contexts an event is returned
250by the method. 347by the method.
251 348
… …
271 ulong IV - Q 368 ulong IV - Q
272 float NV float f 369 float NV float f
273 half IV ushort S 370 half IV ushort S
274 double NV double d 371 double NV double d
275 372
373=head2 GLX SUPPORT
374
375Due to the sad state that OpenGL support is in in Perl (mostly the OpenGL
376module, which has little to no documentation and has little to no support
377for glX), this module, as a special extension, treats context creation
378properties C<OpenCL::GLX_DISPLAY_KHR> and C<OpenCL::GL_CONTEXT_KHR>
379specially: If either or both of these are C<undef>, then the OpenCL
380module tries to dynamically resolve C<glXGetCurrentDisplay> and
381C<glXGetCurrentContext>, call these functions and use their return values
382instead.
383
384For this to work, the OpenGL library must be loaded, a GLX context must
385have been created and be made current, and C<dlsym> must be available and
386capable of finding the function via C<RTLD_DEFAULT>.
387
276=head2 THE OpenCL PACKAGE 388=head2 THE OpenCL PACKAGE
277 389
278=over 4 390=over 4
279 391
280=item $int = OpenCL::errno 392=item $int = OpenCL::errno
… …
286 398
287Comverts an error value into a human readable string. 399Comverts an error value into a human readable string.
288 400
289=item $str = OpenCL::enum2str $enum 401=item $str = OpenCL::enum2str $enum
290 402
291Converts most enum values (inof parameter names, image format constants, 403Converts most enum values (of parameter names, image format constants,
292object types, addressing and filter modes, command types etc.) into a 404object types, addressing and filter modes, command types etc.) into a
293human readbale string. When confronted with some random integer it can be 405human readable string. When confronted with some random integer it can be
294very helpful to pass it through this function to maybe get some readable 406very helpful to pass it through this function to maybe get some readable
295string out of it. 407string out of it.
296 408
297=item @platforms = OpenCL::platforms 409=item @platforms = OpenCL::platforms
298 410
… …
326 438
327Tries to create a context. Never worked for me, and you need devices explicitly anyway. 439Tries to create a context. Never worked for me, and you need devices explicitly anyway.
328 440
329L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html> 441L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>
330 442
331=item $ctx = $device->context ($properties = undef, @$devices, $notify = undef) 443=item $ctx = $platform->context ($properties = undef, @$devices, $notify = undef)
332 444
333Create a new OpenCL::Context object using the given device object(s)- a 445Create a new OpenCL::Context object using the given device object(s)- a
334CL_CONTEXT_PLATFORM property is supplied automatically. 446CL_CONTEXT_PLATFORM property is supplied automatically.
335 447
336L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html> 448L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>
… …
348 460
349=for gengetinfo begin platform 461=for gengetinfo begin platform
350 462
351=item $string = $platform->profile 463=item $string = $platform->profile
352 464
353Calls C<clGetPlatformInfo> with C<CL_PLATFORM_PROFILE> and returns the result(s). 465Calls C<clGetPlatformInfo> with C<CL_PLATFORM_PROFILE> and returns the result.
354 466
355=item $string = $platform->version 467=item $string = $platform->version
356 468
357Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VERSION> and returns the result(s). 469Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VERSION> and returns the result.
358 470
359=item $string = $platform->name 471=item $string = $platform->name
360 472
361Calls C<clGetPlatformInfo> with C<CL_PLATFORM_NAME> and returns the result(s). 473Calls C<clGetPlatformInfo> with C<CL_PLATFORM_NAME> and returns the result.
362 474
363=item $string = $platform->vendor 475=item $string = $platform->vendor
364 476
365Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VENDOR> and returns the result(s). 477Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VENDOR> and returns the result.
366 478
367=item $string = $platform->extensions 479=item $string = $platform->extensions
368 480
369Calls C<clGetPlatformInfo> with C<CL_PLATFORM_EXTENSIONS> and returns the result(s). 481Calls C<clGetPlatformInfo> with C<CL_PLATFORM_EXTENSIONS> and returns the result.
370 482
371=for gengetinfo end platform 483=for gengetinfo end platform
372 484
373=back 485=back
374 486
… …
384 496
385=for gengetinfo begin device 497=for gengetinfo begin device
386 498
387=item $device_type = $device->type 499=item $device_type = $device->type
388 500
389Calls C<clGetDeviceInfo> with C<CL_DEVICE_TYPE> and returns the result(s). 501Calls C<clGetDeviceInfo> with C<CL_DEVICE_TYPE> and returns the result.
390 502
391=item $uint = $device->vendor_id 503=item $uint = $device->vendor_id
392 504
393Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR_ID> and returns the result(s). 505Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR_ID> and returns the result.
394 506
395=item $uint = $device->max_compute_units 507=item $uint = $device->max_compute_units
396 508
397Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_COMPUTE_UNITS> and returns the result(s). 509Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_COMPUTE_UNITS> and returns the result.
398 510
399=item $uint = $device->max_work_item_dimensions 511=item $uint = $device->max_work_item_dimensions
400 512
401Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS> and returns the result(s). 513Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS> and returns the result.
402 514
403=item $int = $device->max_work_group_size 515=item $int = $device->max_work_group_size
404 516
405Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_GROUP_SIZE> and returns the result(s). 517Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_GROUP_SIZE> and returns the result.
406 518
407=item @ints = $device->max_work_item_sizes 519=item @ints = $device->max_work_item_sizes
408 520
409Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_SIZES> and returns the result(s). 521Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_SIZES> and returns the result.
410 522
411=item $uint = $device->preferred_vector_width_char 523=item $uint = $device->preferred_vector_width_char
412 524
413Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR> and returns the result(s). 525Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR> and returns the result.
414 526
415=item $uint = $device->preferred_vector_width_short 527=item $uint = $device->preferred_vector_width_short
416 528
417Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT> and returns the result(s). 529Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT> and returns the result.
418 530
419=item $uint = $device->preferred_vector_width_int 531=item $uint = $device->preferred_vector_width_int
420 532
421Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT> and returns the result(s). 533Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT> and returns the result.
422 534
423=item $uint = $device->preferred_vector_width_long 535=item $uint = $device->preferred_vector_width_long
424 536
425Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG> and returns the result(s). 537Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG> and returns the result.
426 538
427=item $uint = $device->preferred_vector_width_float 539=item $uint = $device->preferred_vector_width_float
428 540
429Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT> and returns the result(s). 541Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT> and returns the result.
430 542
431=item $uint = $device->preferred_vector_width_double 543=item $uint = $device->preferred_vector_width_double
432 544
433Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE> and returns the result(s). 545Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE> and returns the result.
434 546
435=item $uint = $device->max_clock_frequency 547=item $uint = $device->max_clock_frequency
436 548
437Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CLOCK_FREQUENCY> and returns the result(s). 549Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CLOCK_FREQUENCY> and returns the result.
438 550
439=item $bitfield = $device->address_bits 551=item $bitfield = $device->address_bits
440 552
441Calls C<clGetDeviceInfo> with C<CL_DEVICE_ADDRESS_BITS> and returns the result(s). 553Calls C<clGetDeviceInfo> with C<CL_DEVICE_ADDRESS_BITS> and returns the result.
442 554
443=item $uint = $device->max_read_image_args 555=item $uint = $device->max_read_image_args
444 556
445Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_READ_IMAGE_ARGS> and returns the result(s). 557Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_READ_IMAGE_ARGS> and returns the result.
446 558
447=item $uint = $device->max_write_image_args 559=item $uint = $device->max_write_image_args
448 560
449Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WRITE_IMAGE_ARGS> and returns the result(s). 561Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WRITE_IMAGE_ARGS> and returns the result.
450 562
451=item $ulong = $device->max_mem_alloc_size 563=item $ulong = $device->max_mem_alloc_size
452 564
453Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_MEM_ALLOC_SIZE> and returns the result(s). 565Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_MEM_ALLOC_SIZE> and returns the result.
454 566
455=item $int = $device->image2d_max_width 567=item $int = $device->image2d_max_width
456 568
457Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_WIDTH> and returns the result(s). 569Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_WIDTH> and returns the result.
458 570
459=item $int = $device->image2d_max_height 571=item $int = $device->image2d_max_height
460 572
461Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_HEIGHT> and returns the result(s). 573Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_HEIGHT> and returns the result.
462 574
463=item $int = $device->image3d_max_width 575=item $int = $device->image3d_max_width
464 576
465Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_WIDTH> and returns the result(s). 577Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_WIDTH> and returns the result.
466 578
467=item $int = $device->image3d_max_height 579=item $int = $device->image3d_max_height
468 580
469Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_HEIGHT> and returns the result(s). 581Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_HEIGHT> and returns the result.
470 582
471=item $int = $device->image3d_max_depth 583=item $int = $device->image3d_max_depth
472 584
473Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_DEPTH> and returns the result(s). 585Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_DEPTH> and returns the result.
474 586
475=item $uint = $device->image_support 587=item $uint = $device->image_support
476 588
477Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE_SUPPORT> and returns the result(s). 589Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE_SUPPORT> and returns the result.
478 590
479=item $int = $device->max_parameter_size 591=item $int = $device->max_parameter_size
480 592
481Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_PARAMETER_SIZE> and returns the result(s). 593Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_PARAMETER_SIZE> and returns the result.
482 594
483=item $uint = $device->max_samplers 595=item $uint = $device->max_samplers
484 596
485Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_SAMPLERS> and returns the result(s). 597Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_SAMPLERS> and returns the result.
486 598
487=item $uint = $device->mem_base_addr_align 599=item $uint = $device->mem_base_addr_align
488 600
489Calls C<clGetDeviceInfo> with C<CL_DEVICE_MEM_BASE_ADDR_ALIGN> and returns the result(s). 601Calls C<clGetDeviceInfo> with C<CL_DEVICE_MEM_BASE_ADDR_ALIGN> and returns the result.
490 602
491=item $uint = $device->min_data_type_align_size 603=item $uint = $device->min_data_type_align_size
492 604
493Calls C<clGetDeviceInfo> with C<CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE> and returns the result(s). 605Calls C<clGetDeviceInfo> with C<CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE> and returns the result.
494 606
495=item $device_fp_config = $device->single_fp_config 607=item $device_fp_config = $device->single_fp_config
496 608
497Calls C<clGetDeviceInfo> with C<CL_DEVICE_SINGLE_FP_CONFIG> and returns the result(s). 609Calls C<clGetDeviceInfo> with C<CL_DEVICE_SINGLE_FP_CONFIG> and returns the result.
498 610
499=item $device_mem_cache_type = $device->global_mem_cache_type 611=item $device_mem_cache_type = $device->global_mem_cache_type
500 612
501Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_TYPE> and returns the result(s). 613Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_TYPE> and returns the result.
502 614
503=item $uint = $device->global_mem_cacheline_size 615=item $uint = $device->global_mem_cacheline_size
504 616
505Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE> and returns the result(s). 617Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE> and returns the result.
506 618
507=item $ulong = $device->global_mem_cache_size 619=item $ulong = $device->global_mem_cache_size
508 620
509Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_SIZE> and returns the result(s). 621Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_SIZE> and returns the result.
510 622
511=item $ulong = $device->global_mem_size 623=item $ulong = $device->global_mem_size
512 624
513Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_SIZE> and returns the result(s). 625Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_SIZE> and returns the result.
514 626
515=item $ulong = $device->max_constant_buffer_size 627=item $ulong = $device->max_constant_buffer_size
516 628
517Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE> and returns the result(s). 629Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE> and returns the result.
518 630
519=item $uint = $device->max_constant_args 631=item $uint = $device->max_constant_args
520 632
521Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_ARGS> and returns the result(s). 633Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_ARGS> and returns the result.
522 634
523=item $device_local_mem_type = $device->local_mem_type 635=item $device_local_mem_type = $device->local_mem_type
524 636
525Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_TYPE> and returns the result(s). 637Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_TYPE> and returns the result.
526 638
527=item $ulong = $device->local_mem_size 639=item $ulong = $device->local_mem_size
528 640
529Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_SIZE> and returns the result(s). 641Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_SIZE> and returns the result.
530 642
531=item $boolean = $device->error_correction_support 643=item $boolean = $device->error_correction_support
532 644
533Calls C<clGetDeviceInfo> with C<CL_DEVICE_ERROR_CORRECTION_SUPPORT> and returns the result(s). 645Calls C<clGetDeviceInfo> with C<CL_DEVICE_ERROR_CORRECTION_SUPPORT> and returns the result.
534 646
535=item $int = $device->profiling_timer_resolution 647=item $int = $device->profiling_timer_resolution
536 648
537Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILING_TIMER_RESOLUTION> and returns the result(s). 649Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILING_TIMER_RESOLUTION> and returns the result.
538 650
539=item $boolean = $device->endian_little 651=item $boolean = $device->endian_little
540 652
541Calls C<clGetDeviceInfo> with C<CL_DEVICE_ENDIAN_LITTLE> and returns the result(s). 653Calls C<clGetDeviceInfo> with C<CL_DEVICE_ENDIAN_LITTLE> and returns the result.
542 654
543=item $boolean = $device->available 655=item $boolean = $device->available
544 656
545Calls C<clGetDeviceInfo> with C<CL_DEVICE_AVAILABLE> and returns the result(s). 657Calls C<clGetDeviceInfo> with C<CL_DEVICE_AVAILABLE> and returns the result.
546 658
547=item $boolean = $device->compiler_available 659=item $boolean = $device->compiler_available
548 660
549Calls C<clGetDeviceInfo> with C<CL_DEVICE_COMPILER_AVAILABLE> and returns the result(s). 661Calls C<clGetDeviceInfo> with C<CL_DEVICE_COMPILER_AVAILABLE> and returns the result.
550 662
551=item $device_exec_capabilities = $device->execution_capabilities 663=item $device_exec_capabilities = $device->execution_capabilities
552 664
553Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXECUTION_CAPABILITIES> and returns the result(s). 665Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXECUTION_CAPABILITIES> and returns the result.
554 666
555=item $command_queue_properties = $device->properties 667=item $command_queue_properties = $device->properties
556 668
557Calls C<clGetDeviceInfo> with C<CL_DEVICE_QUEUE_PROPERTIES> and returns the result(s). 669Calls C<clGetDeviceInfo> with C<CL_DEVICE_QUEUE_PROPERTIES> and returns the result.
558 670
559=item $ = $device->platform 671=item $ = $device->platform
560 672
561Calls C<clGetDeviceInfo> with C<CL_DEVICE_PLATFORM> and returns the result(s). 673Calls C<clGetDeviceInfo> with C<CL_DEVICE_PLATFORM> and returns the result.
562 674
563=item $string = $device->name 675=item $string = $device->name
564 676
565Calls C<clGetDeviceInfo> with C<CL_DEVICE_NAME> and returns the result(s). 677Calls C<clGetDeviceInfo> with C<CL_DEVICE_NAME> and returns the result.
566 678
567=item $string = $device->vendor 679=item $string = $device->vendor
568 680
569Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR> and returns the result(s). 681Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR> and returns the result.
570 682
571=item $string = $device->driver_version 683=item $string = $device->driver_version
572 684
573Calls C<clGetDeviceInfo> with C<CL_DRIVER_VERSION> and returns the result(s). 685Calls C<clGetDeviceInfo> with C<CL_DRIVER_VERSION> and returns the result.
574 686
575=item $string = $device->profile 687=item $string = $device->profile
576 688
577Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILE> and returns the result(s). 689Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILE> and returns the result.
578 690
579=item $string = $device->version 691=item $string = $device->version
580 692
581Calls C<clGetDeviceInfo> with C<CL_DEVICE_VERSION> and returns the result(s). 693Calls C<clGetDeviceInfo> with C<CL_DEVICE_VERSION> and returns the result.
582 694
583=item $string = $device->extensions 695=item $string = $device->extensions
584 696
585Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXTENSIONS> and returns the result(s). 697Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXTENSIONS> and returns the result.
586 698
587=item $uint = $device->preferred_vector_width_half 699=item $uint = $device->preferred_vector_width_half
588 700
589Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF> and returns the result(s). 701Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF> and returns the result.
590 702
591=item $uint = $device->native_vector_width_char 703=item $uint = $device->native_vector_width_char
592 704
593Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR> and returns the result(s). 705Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR> and returns the result.
594 706
595=item $uint = $device->native_vector_width_short 707=item $uint = $device->native_vector_width_short
596 708
597Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT> and returns the result(s). 709Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT> and returns the result.
598 710
599=item $uint = $device->native_vector_width_int 711=item $uint = $device->native_vector_width_int
600 712
601Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_INT> and returns the result(s). 713Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_INT> and returns the result.
602 714
603=item $uint = $device->native_vector_width_long 715=item $uint = $device->native_vector_width_long
604 716
605Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG> and returns the result(s). 717Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG> and returns the result.
606 718
607=item $uint = $device->native_vector_width_float 719=item $uint = $device->native_vector_width_float
608 720
609Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT> and returns the result(s). 721Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT> and returns the result.
610 722
611=item $uint = $device->native_vector_width_double 723=item $uint = $device->native_vector_width_double
612 724
613Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE> and returns the result(s). 725Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE> and returns the result.
614 726
615=item $uint = $device->native_vector_width_half 727=item $uint = $device->native_vector_width_half
616 728
617Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF> and returns the result(s). 729Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF> and returns the result.
618 730
619=item $device_fp_config = $device->double_fp_config 731=item $device_fp_config = $device->double_fp_config
620 732
621Calls C<clGetDeviceInfo> with C<CL_DEVICE_DOUBLE_FP_CONFIG> and returns the result(s). 733Calls C<clGetDeviceInfo> with C<CL_DEVICE_DOUBLE_FP_CONFIG> and returns the result.
622 734
623=item $device_fp_config = $device->half_fp_config 735=item $device_fp_config = $device->half_fp_config
624 736
625Calls C<clGetDeviceInfo> with C<CL_DEVICE_HALF_FP_CONFIG> and returns the result(s). 737Calls C<clGetDeviceInfo> with C<CL_DEVICE_HALF_FP_CONFIG> and returns the result.
626 738
627=item $boolean = $device->host_unified_memory 739=item $boolean = $device->host_unified_memory
628 740
629Calls C<clGetDeviceInfo> with C<CL_DEVICE_HOST_UNIFIED_MEMORY> and returns the result(s). 741Calls C<clGetDeviceInfo> with C<CL_DEVICE_HOST_UNIFIED_MEMORY> and returns the result.
630 742
631=item $device = $device->parent_device_ext 743=item $device = $device->parent_device_ext
632 744
633Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARENT_DEVICE_EXT> and returns the result(s). 745Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARENT_DEVICE_EXT> and returns the result.
634 746
635=item @device_partition_property_exts = $device->partition_types_ext 747=item @device_partition_property_exts = $device->partition_types_ext
636 748
637Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_TYPES_EXT> and returns the result(s). 749Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_TYPES_EXT> and returns the result.
638 750
639=item @device_partition_property_exts = $device->affinity_domains_ext 751=item @device_partition_property_exts = $device->affinity_domains_ext
640 752
641Calls C<clGetDeviceInfo> with C<CL_DEVICE_AFFINITY_DOMAINS_EXT> and returns the result(s). 753Calls C<clGetDeviceInfo> with C<CL_DEVICE_AFFINITY_DOMAINS_EXT> and returns the result.
642 754
643=item $uint = $device->reference_count_ext 755=item $uint = $device->reference_count_ext
644 756
645Calls C<clGetDeviceInfo> with C<CL_DEVICE_REFERENCE_COUNT_EXT > and returns the result(s). 757Calls C<clGetDeviceInfo> with C<CL_DEVICE_REFERENCE_COUNT_EXT> and returns the result.
646 758
647=item @device_partition_property_exts = $device->partition_style_ext 759=item @device_partition_property_exts = $device->partition_style_ext
648 760
649Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_STYLE_EXT> and returns the result(s). 761Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_STYLE_EXT> and returns the result.
650 762
651=for gengetinfo end device 763=for gengetinfo end device
652 764
653=back 765=back
654 766
… …
660 772
661Create a new OpenCL::Queue object from the context and the given device. 773Create a new OpenCL::Queue object from the context and the given device.
662 774
663L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateCommandQueue.html> 775L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateCommandQueue.html>
664 776
777Example: create an out-of-order queue.
778
779 $queue = $ctx->queue ($device, OpenCL::QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE);
780
665=item $ev = $ctx->user_event 781=item $ev = $ctx->user_event
666 782
667Creates a new OpenCL::UserEvent object. 783Creates a new OpenCL::UserEvent object.
668 784
669L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateUserEvent.html> 785L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateUserEvent.html>
670 786
671=item $buf = $ctx->buffer ($flags, $len) 787=item $buf = $ctx->buffer ($flags, $len)
672 788
673Creates a new OpenCL::Buffer object with the given flags and octet-size. 789Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object with the
790given flags and octet-size.
674 791
675L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateBuffer.html> 792L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateBuffer.html>
676 793
677=item $buf = $ctx->buffer_sv ($flags, $data) 794=item $buf = $ctx->buffer_sv ($flags, $data)
678 795
679Creates a new OpenCL::Buffer object and initialise it with the given data values. 796Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object and
797initialise it with the given data values.
798
799=item $img = $ctx->image ($self, $flags, $channel_order, $channel_type, $type, $width, $height, $depth, $array_size = 0, $row_pitch = 0, $slice_pitch = 0, $num_mip_level = 0, $num_samples = 0, $*data = &PL_sv_undef)
800
801Creates a new OpenCL::Image object and optionally initialises it with
802the given data values.
803
804L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateImage.html>
680 805
681=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef) 806=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef)
682 807
683Creates a new OpenCL::Image2D object and optionally initialises it with the given data values. 808Creates a new OpenCL::Image2D object and optionally initialises it with
809the given data values.
684 810
685L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage2D.html> 811L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage2D.html>
686 812
687=item $img = $ctx->image3d ($flags, $channel_order, $channel_type, $width, $height, $depth, $row_pitch = 0, $slice_pitch = 0, $data = undef) 813=item $img = $ctx->image3d ($flags, $channel_order, $channel_type, $width, $height, $depth, $row_pitch = 0, $slice_pitch = 0, $data = undef)
688 814
689Creates a new OpenCL::Image3D object and optionally initialises it with the given data values. 815Creates a new OpenCL::Image3D object and optionally initialises it with
816the given data values.
690 817
691L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage3D.html> 818L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage3D.html>
819
820=item $buffer = $ctx->gl_buffer ($flags, $bufobj)
821
822Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object that refers to the given
823OpenGL buffer object.
824
825http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLBuffer.html
826
827=item $img = $ctx->gl_texture ($flags, $target, $miplevel, $texture)
828
829Creates a new OpenCL::Image object that refers to the given OpenGL
830texture object or buffer.
831
832http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateFromGLTexture.html
833
834=item $img = $ctx->gl_texture2d ($flags, $target, $miplevel, $texture)
835
836Creates a new OpenCL::Image2D object that refers to the given OpenGL
8372D texture object.
838
839http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture2D.html
840
841=item $img = $ctx->gl_texture3d ($flags, $target, $miplevel, $texture)
842
843Creates a new OpenCL::Image3D object that refers to the given OpenGL
8443D texture object.
845
846http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture3D.html
847
848=item $ctx->gl_renderbuffer ($flags, $renderbuffer)
849
850Creates a new OpenCL::Image2D object that refers to the given OpenGL
851render buffer.
852
853http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLRenderbuffer.html
692 854
693=item @formats = $ctx->supported_image_formats ($flags, $image_type) 855=item @formats = $ctx->supported_image_formats ($flags, $image_type)
694 856
695Returns a list of matching image formats - each format is an arrayref with 857Returns a list of matching image formats - each format is an arrayref with
696two values, $channel_order and $channel_type, in it. 858two values, $channel_order and $channel_type, in it.
… …
717 879
718=for gengetinfo begin context 880=for gengetinfo begin context
719 881
720=item $uint = $context->reference_count 882=item $uint = $context->reference_count
721 883
722Calls C<clGetContextInfo> with C<CL_CONTEXT_REFERENCE_COUNT> and returns the result(s). 884Calls C<clGetContextInfo> with C<CL_CONTEXT_REFERENCE_COUNT> and returns the result.
723 885
724=item @devices = $context->devices 886=item @devices = $context->devices
725 887
726Calls C<clGetContextInfo> with C<CL_CONTEXT_DEVICES> and returns the result(s). 888Calls C<clGetContextInfo> with C<CL_CONTEXT_DEVICES> and returns the result.
727 889
728=item @property_ints = $context->properties 890=item @property_ints = $context->properties
729 891
730Calls C<clGetContextInfo> with C<CL_CONTEXT_PROPERTIES> and returns the result(s). 892Calls C<clGetContextInfo> with C<CL_CONTEXT_PROPERTIES> and returns the result.
731 893
732=item $uint = $context->num_devices 894=item $uint = $context->num_devices
733 895
734Calls C<clGetContextInfo> with C<CL_CONTEXT_NUM_DEVICES> and returns the result(s). 896Calls C<clGetContextInfo> with C<CL_CONTEXT_NUM_DEVICES> and returns the result.
735 897
736=for gengetinfo end context 898=for gengetinfo end context
737 899
738=back 900=back
739 901
… …
747for completion, unless the method is called in void context, in which case 909for completion, unless the method is called in void context, in which case
748no event object is created. 910no event object is created.
749 911
750They also allow you to specify any number of other event objects that this 912They also allow you to specify any number of other event objects that this
751request has to wait for before it starts executing, by simply passing the 913request has to wait for before it starts executing, by simply passing the
752event objects as extra parameters to the enqueue methods. 914event objects as extra parameters to the enqueue methods. To simplify
915program design, this module ignores any C<undef> values in the list of
916events. This makes it possible to code operations such as this, without
917having to put a valid event object into C<$event> first:
918
919 $event = $queue->enqueue_xxx (..., $event);
753 920
754Queues execute in-order by default, without any parallelism, so in most 921Queues execute in-order by default, without any parallelism, so in most
755cases (i.e. you use only one queue) it's not necessary to wait for or 922cases (i.e. you use only one queue) it's not necessary to wait for or
756create event objects. 923create event objects, althoguh an our of order queue is often a bit
924faster.
757 925
758=over 4 926=over 4
759 927
760=item $ev = $queue->enqueue_read_buffer ($buffer, $blocking, $offset, $len, $data, $wait_events...) 928=item $ev = $queue->enqueue_read_buffer ($buffer, $blocking, $offset, $len, $data, $wait_events...)
761 929
… …
771 939
772=item $ev = $queue->enqueue_copy_buffer ($src, $dst, $src_offset, $dst_offset, $len, $wait_events...) 940=item $ev = $queue->enqueue_copy_buffer ($src, $dst, $src_offset, $dst_offset, $len, $wait_events...)
773 941
774L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBuffer.html> 942L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBuffer.html>
775 943
944=item $ev = $queue->enqueue_read_buffer_rect (OpenCL::Memory buf, cl_bool blocking, $buf_x, $buf_y, $buf_z, $host_x, $host_y, $host_z, $width, $height, $depth, $buf_row_pitch, $buf_slice_pitch, $host_row_pitch, $host_slice_pitch, $data, $wait_events...)
945
946http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadBufferRect.html
947
948=item $ev = $queue->enqueue_write_buffer_rect (OpenCL::Memory buf, cl_bool blocking, $buf_x, $buf_y, $buf_z, $host_x, $host_y, $host_z, $width, $height, $depth, $buf_row_pitch, $buf_slice_pitch, $host_row_pitch, $host_slice_pitch, $data, $wait_events...)
949
950http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteBufferRect.html
951
776=item $ev = $queue->enqueue_read_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...) 952=item $ev = $queue->enqueue_read_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...)
777 953
954L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferRect.html>
955
956=item $ev = $queue->enqueue_copy_buffer_to_image ($src_buffer, $dst_image, $src_offset, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $wait_events...)
957
778L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadImage.html> 958L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadImage.html>
779 959
780=item $ev = $queue->enqueue_write_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...) 960=item $ev = $queue->enqueue_write_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...)
781 961
782L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteImage.html> 962L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteImage.html>
783 963
964=item $ev = $queue->enqueue_copy_image ($src_image, $dst_image, $src_x, $src_y, $src_z, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $wait_events...)
965
966L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImage.html>
967
968=item $ev = $queue->enqueue_copy_image_to_buffer ($src_image, $dst_image, $src_x, $src_y, $src_z, $width, $height, $depth, $dst_offset, $wait_events...)
969
970L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImageToBuffer.html>
971
784=item $ev = $queue->enqueue_copy_buffer_rect ($src, $dst, $src_x, $src_y, $src_z, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $src_row_pitch, $src_slice_pitch, $dst_row_pitch, $dst_slice_pitch, $wait_event...) 972=item $ev = $queue->enqueue_copy_buffer_rect ($src, $dst, $src_x, $src_y, $src_z, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $src_row_pitch, $src_slice_pitch, $dst_row_pitch, $dst_slice_pitch, $wait_event...)
785 973
786Yeah. 974Yeah.
787 975
788L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferRect.html>
789
790=item $ev = $queue->enqueue_copy_buffer_to_image ($src_buffer, $dst_image, $src_offset, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $wait_events...)
791
792L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferToImage.html>. 976L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferToImage.html>.
793
794=item $ev = $queue->enqueue_copy_image ($src_image, $dst_image, $src_x, $src_y, $src_z, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $wait_events...)
795
796L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImage.html>
797
798=item $ev = $queue->enqueue_copy_image_to_buffer ($src_image, $dst_image, $src_x, $src_y, $src_z, $width, $height, $depth, $dst_offset, $wait_events...)
799
800L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImageToBuffer.html>
801 977
802=item $ev = $queue->enqueue_task ($kernel, $wait_events...) 978=item $ev = $queue->enqueue_task ($kernel, $wait_events...)
803 979
804L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueTask.html> 980L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueTask.html>
805 981
… …
819reference to an array of local work sizes, with the same number of 995reference to an array of local work sizes, with the same number of
820elements as @$global_work_size. 996elements as @$global_work_size.
821 997
822L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html> 998L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html>
823 999
824=item $ev = $queue->enqueue_marker 1000=item $ev = $queue->enqueue_acquire_gl_objects ([object, ...], $wait_events...)
825 1001
1002Enqueues a list (an array-ref of OpenCL::Memory objects) to be acquired
1003for subsequent OpenCL usage.
1004
826L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMarker.html> 1005L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueAcquireGLObjects.html>
1006
1007=item $ev = $queue->enqueue_release_gl_objects ([object, ...], $wait_events...)
1008
1009Enqueues a list (an array-ref of OpenCL::Memory objects) to be released
1010for subsequent OpenGL usage.
1011
1012L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReleaseGLObjects.html>
827 1013
828=item $ev = $queue->enqueue_wait_for_events ($wait_events...) 1014=item $ev = $queue->enqueue_wait_for_events ($wait_events...)
829 1015
830L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWaitForEvents.html> 1016L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWaitForEvents.html>
831 1017
832=item $queue->enqueue_barrier 1018=item $ev = $queue->enqueue_marker ($wait_events...)
833 1019
1020L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueMarkerWithWaitList.html>
1021
1022=item $ev = $queue->enqueue_barrier ($wait_events...)
1023
834L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueBarrier.html> 1024L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueBarrierWithWaitList.html>
835 1025
836=item $queue->flush 1026=item $queue->flush
837 1027
838L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFlush.html> 1028L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFlush.html>
839 1029
… …
849 1039
850=for gengetinfo begin command_queue 1040=for gengetinfo begin command_queue
851 1041
852=item $ctx = $command_queue->context 1042=item $ctx = $command_queue->context
853 1043
854Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_CONTEXT> and returns the result(s). 1044Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_CONTEXT> and returns the result.
855 1045
856=item $device = $command_queue->device 1046=item $device = $command_queue->device
857 1047
858Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_DEVICE> and returns the result(s). 1048Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_DEVICE> and returns the result.
859 1049
860=item $uint = $command_queue->reference_count 1050=item $uint = $command_queue->reference_count
861 1051
862Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_REFERENCE_COUNT> and returns the result(s). 1052Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_REFERENCE_COUNT> and returns the result.
863 1053
864=item $command_queue_properties = $command_queue->properties 1054=item $command_queue_properties = $command_queue->properties
865 1055
866Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_PROPERTIES> and returns the result(s). 1056Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_PROPERTIES> and returns the result.
867 1057
868=for gengetinfo end command_queue 1058=for gengetinfo end command_queue
869 1059
870=back 1060=back
871 1061
… …
884 1074
885=for gengetinfo begin mem 1075=for gengetinfo begin mem
886 1076
887=item $mem_object_type = $mem->type 1077=item $mem_object_type = $mem->type
888 1078
889Calls C<clGetMemObjectInfo> with C<CL_MEM_TYPE> and returns the result(s). 1079Calls C<clGetMemObjectInfo> with C<CL_MEM_TYPE> and returns the result.
890 1080
891=item $mem_flags = $mem->flags 1081=item $mem_flags = $mem->flags
892 1082
893Calls C<clGetMemObjectInfo> with C<CL_MEM_FLAGS> and returns the result(s). 1083Calls C<clGetMemObjectInfo> with C<CL_MEM_FLAGS> and returns the result.
894 1084
895=item $int = $mem->size 1085=item $int = $mem->size
896 1086
897Calls C<clGetMemObjectInfo> with C<CL_MEM_SIZE> and returns the result(s). 1087Calls C<clGetMemObjectInfo> with C<CL_MEM_SIZE> and returns the result.
898 1088
899=item $ptr_value = $mem->host_ptr 1089=item $ptr_value = $mem->host_ptr
900 1090
901Calls C<clGetMemObjectInfo> with C<CL_MEM_HOST_PTR> and returns the result(s). 1091Calls C<clGetMemObjectInfo> with C<CL_MEM_HOST_PTR> and returns the result.
902 1092
903=item $uint = $mem->map_count 1093=item $uint = $mem->map_count
904 1094
905Calls C<clGetMemObjectInfo> with C<CL_MEM_MAP_COUNT> and returns the result(s). 1095Calls C<clGetMemObjectInfo> with C<CL_MEM_MAP_COUNT> and returns the result.
906 1096
907=item $uint = $mem->reference_count 1097=item $uint = $mem->reference_count
908 1098
909Calls C<clGetMemObjectInfo> with C<CL_MEM_REFERENCE_COUNT> and returns the result(s). 1099Calls C<clGetMemObjectInfo> with C<CL_MEM_REFERENCE_COUNT> and returns the result.
910 1100
911=item $ctx = $mem->context 1101=item $ctx = $mem->context
912 1102
913Calls C<clGetMemObjectInfo> with C<CL_MEM_CONTEXT> and returns the result(s). 1103Calls C<clGetMemObjectInfo> with C<CL_MEM_CONTEXT> and returns the result.
914 1104
915=item $mem = $mem->associated_memobject 1105=item $mem = $mem->associated_memobject
916 1106
917Calls C<clGetMemObjectInfo> with C<CL_MEM_ASSOCIATED_MEMOBJECT> and returns the result(s). 1107Calls C<clGetMemObjectInfo> with C<CL_MEM_ASSOCIATED_MEMOBJECT> and returns the result.
918 1108
919=item $int = $mem->offset 1109=item $int = $mem->offset
920 1110
921Calls C<clGetMemObjectInfo> with C<CL_MEM_OFFSET> and returns the result(s). 1111Calls C<clGetMemObjectInfo> with C<CL_MEM_OFFSET> and returns the result.
922 1112
923=for gengetinfo end mem 1113=for gengetinfo end mem
924 1114
1115=item ($type, $name) = $mem->gl_object_info
1116
1117Returns the OpenGL object type (e.g. OpenCL::GL_OBJECT_TEXTURE2D) and the
1118object "name" (e.g. the texture name) used to create this memory object.
1119
1120L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetGLObjectInfo.html>
1121
925=back 1122=back
926 1123
1124=head2 THE OpenCL::Buffer CLASS
1125
1126This is a subclass of OpenCL::Memory, and the superclass of
1127OpenCL::BufferObj. Its purpose is simply to distinguish between buffers
1128and sub-buffers.
1129
1130=head2 THE OpenCL::BufferObj CLASS
1131
1132This is a subclass of OpenCL::Buffer and thus OpenCL::Memory. It exists
1133because one cna create sub buffers of OpenLC::BufferObj objects, but not
1134sub buffers from these sub buffers.
1135
1136=over 4
1137
1138=item $subbuf = $buf_obj->sub_buffer_region ($flags, $origin, $size)
1139
1140Creates an OpenCL::Buffer objects from this buffer and returns it. The
1141C<buffer_create_type> is assumed to be C<CL_BUFFER_CREATE_TYPE_REGION>.
1142
1143L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSubBuffer.html>
1144
1145=back
1146
927=head2 THE OpenCL::Image CLASS 1147=head2 THE OpenCL::Image CLASS
928 1148
929This is the superclass of all image objects - OpenCL::Image2D and OpenCL::Image3D. 1149This is the superclass of all image objects - OpenCL::Image1D,
1150OpenCL::Image1DArray, OpenCL::Image1DBuffer, OpenCL::Image2D,
1151OpenCL::Image2DArray and OpenCL::Image3D.
930 1152
931=over 4 1153=over 4
932 1154
933=item $packed_value = $ev->image_info ($name) 1155=item $packed_value = $ev->image_info ($name)
934 1156
… …
941 1163
942=for gengetinfo begin image 1164=for gengetinfo begin image
943 1165
944=item $int = $image->element_size 1166=item $int = $image->element_size
945 1167
946Calls C<clGetImageInfo> with C<CL_IMAGE_ELEMENT_SIZE> and returns the result(s). 1168Calls C<clGetImageInfo> with C<CL_IMAGE_ELEMENT_SIZE> and returns the result.
947 1169
948=item $int = $image->row_pitch 1170=item $int = $image->row_pitch
949 1171
950Calls C<clGetImageInfo> with C<CL_IMAGE_ROW_PITCH> and returns the result(s). 1172Calls C<clGetImageInfo> with C<CL_IMAGE_ROW_PITCH> and returns the result.
951 1173
952=item $int = $image->slice_pitch 1174=item $int = $image->slice_pitch
953 1175
954Calls C<clGetImageInfo> with C<CL_IMAGE_SLICE_PITCH> and returns the result(s). 1176Calls C<clGetImageInfo> with C<CL_IMAGE_SLICE_PITCH> and returns the result.
955 1177
956=item $int = $image->width 1178=item $int = $image->width
957 1179
958Calls C<clGetImageInfo> with C<CL_IMAGE_WIDTH> and returns the result(s). 1180Calls C<clGetImageInfo> with C<CL_IMAGE_WIDTH> and returns the result.
959 1181
960=item $int = $image->height 1182=item $int = $image->height
961 1183
962Calls C<clGetImageInfo> with C<CL_IMAGE_HEIGHT> and returns the result(s). 1184Calls C<clGetImageInfo> with C<CL_IMAGE_HEIGHT> and returns the result.
963 1185
964=item $int = $image->depth 1186=item $int = $image->depth
965 1187
966Calls C<clGetImageInfo> with C<CL_IMAGE_DEPTH> and returns the result(s). 1188Calls C<clGetImageInfo> with C<CL_IMAGE_DEPTH> and returns the result.
967 1189
968=for gengetinfo end image 1190=for gengetinfo end image
969 1191
1192=for gengetinfo begin gl_texture
1193
1194=item $GLenum = $gl_texture->target
1195
1196Calls C<clGetGLTextureInfo> with C<CL_GL_TEXTURE_TARGET> and returns the result.
1197
1198=item $GLint = $gl_texture->gl_mipmap_level
1199
1200Calls C<clGetGLTextureInfo> with C<CL_GL_MIPMAP_LEVEL> and returns the result.
1201
1202=for gengetinfo end gl_texture
1203
970=back 1204=back
971 1205
972=head2 THE OpenCL::Sampler CLASS 1206=head2 THE OpenCL::Sampler CLASS
973 1207
974=over 4 1208=over 4
… …
981 1215
982=for gengetinfo begin sampler 1216=for gengetinfo begin sampler
983 1217
984=item $uint = $sampler->reference_count 1218=item $uint = $sampler->reference_count
985 1219
986Calls C<clGetSamplerInfo> with C<CL_SAMPLER_REFERENCE_COUNT> and returns the result(s). 1220Calls C<clGetSamplerInfo> with C<CL_SAMPLER_REFERENCE_COUNT> and returns the result.
987 1221
988=item $ctx = $sampler->context 1222=item $ctx = $sampler->context
989 1223
990Calls C<clGetSamplerInfo> with C<CL_SAMPLER_CONTEXT> and returns the result(s). 1224Calls C<clGetSamplerInfo> with C<CL_SAMPLER_CONTEXT> and returns the result.
991 1225
992=item $addressing_mode = $sampler->normalized_coords 1226=item $addressing_mode = $sampler->normalized_coords
993 1227
994Calls C<clGetSamplerInfo> with C<CL_SAMPLER_NORMALIZED_COORDS> and returns the result(s). 1228Calls C<clGetSamplerInfo> with C<CL_SAMPLER_NORMALIZED_COORDS> and returns the result.
995 1229
996=item $filter_mode = $sampler->addressing_mode 1230=item $filter_mode = $sampler->addressing_mode
997 1231
998Calls C<clGetSamplerInfo> with C<CL_SAMPLER_ADDRESSING_MODE> and returns the result(s). 1232Calls C<clGetSamplerInfo> with C<CL_SAMPLER_ADDRESSING_MODE> and returns the result.
999 1233
1000=item $boolean = $sampler->filter_mode 1234=item $boolean = $sampler->filter_mode
1001 1235
1002Calls C<clGetSamplerInfo> with C<CL_SAMPLER_FILTER_MODE> and returns the result(s). 1236Calls C<clGetSamplerInfo> with C<CL_SAMPLER_FILTER_MODE> and returns the result.
1003 1237
1004=for gengetinfo end sampler 1238=for gengetinfo end sampler
1005 1239
1006=back 1240=back
1007 1241
… …
1031 1265
1032=for gengetinfo begin program_build 1266=for gengetinfo begin program_build
1033 1267
1034=item $build_status = $program->build_status ($device) 1268=item $build_status = $program->build_status ($device)
1035 1269
1036Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_STATUS> and returns the result(s). 1270Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_STATUS> and returns the result.
1037 1271
1038=item $string = $program->build_options ($device) 1272=item $string = $program->build_options ($device)
1039 1273
1040Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_OPTIONS> and returns the result(s). 1274Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_OPTIONS> and returns the result.
1041 1275
1042=item $string = $program->build_log ($device) 1276=item $string = $program->build_log ($device)
1043 1277
1044Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_LOG> and returns the result(s). 1278Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_LOG> and returns the result.
1045 1279
1046=for gengetinfo end program_build 1280=for gengetinfo end program_build
1047 1281
1048=item $packed_value = $program->info ($name) 1282=item $packed_value = $program->info ($name)
1049 1283
… …
1053 1287
1054=for gengetinfo begin program 1288=for gengetinfo begin program
1055 1289
1056=item $uint = $program->reference_count 1290=item $uint = $program->reference_count
1057 1291
1058Calls C<clGetProgramInfo> with C<CL_PROGRAM_REFERENCE_COUNT> and returns the result(s). 1292Calls C<clGetProgramInfo> with C<CL_PROGRAM_REFERENCE_COUNT> and returns the result.
1059 1293
1060=item $ctx = $program->context 1294=item $ctx = $program->context
1061 1295
1062Calls C<clGetProgramInfo> with C<CL_PROGRAM_CONTEXT> and returns the result(s). 1296Calls C<clGetProgramInfo> with C<CL_PROGRAM_CONTEXT> and returns the result.
1063 1297
1064=item $uint = $program->num_devices 1298=item $uint = $program->num_devices
1065 1299
1066Calls C<clGetProgramInfo> with C<CL_PROGRAM_NUM_DEVICES> and returns the result(s). 1300Calls C<clGetProgramInfo> with C<CL_PROGRAM_NUM_DEVICES> and returns the result.
1067 1301
1068=item @devices = $program->devices 1302=item @devices = $program->devices
1069 1303
1070Calls C<clGetProgramInfo> with C<CL_PROGRAM_DEVICES> and returns the result(s). 1304Calls C<clGetProgramInfo> with C<CL_PROGRAM_DEVICES> and returns the result.
1071 1305
1072=item $string = $program->source 1306=item $string = $program->source
1073 1307
1074Calls C<clGetProgramInfo> with C<CL_PROGRAM_SOURCE> and returns the result(s). 1308Calls C<clGetProgramInfo> with C<CL_PROGRAM_SOURCE> and returns the result.
1075 1309
1076=item @ints = $program->binary_sizes 1310=item @ints = $program->binary_sizes
1077 1311
1078Calls C<clGetProgramInfo> with C<CL_PROGRAM_BINARY_SIZES> and returns the result(s). 1312Calls C<clGetProgramInfo> with C<CL_PROGRAM_BINARY_SIZES> and returns the result.
1079 1313
1080=for gengetinfo end program 1314=for gengetinfo end program
1081 1315
1082=item @blobs = $program->binaries 1316=item @blobs = $program->binaries
1083 1317
… …
1104 1338
1105=for gengetinfo begin kernel 1339=for gengetinfo begin kernel
1106 1340
1107=item $string = $kernel->function_name 1341=item $string = $kernel->function_name
1108 1342
1109Calls C<clGetKernelInfo> with C<CL_KERNEL_FUNCTION_NAME> and returns the result(s). 1343Calls C<clGetKernelInfo> with C<CL_KERNEL_FUNCTION_NAME> and returns the result.
1110 1344
1111=item $uint = $kernel->num_args 1345=item $uint = $kernel->num_args
1112 1346
1113Calls C<clGetKernelInfo> with C<CL_KERNEL_NUM_ARGS> and returns the result(s). 1347Calls C<clGetKernelInfo> with C<CL_KERNEL_NUM_ARGS> and returns the result.
1114 1348
1115=item $uint = $kernel->reference_count 1349=item $uint = $kernel->reference_count
1116 1350
1117Calls C<clGetKernelInfo> with C<CL_KERNEL_REFERENCE_COUNT> and returns the result(s). 1351Calls C<clGetKernelInfo> with C<CL_KERNEL_REFERENCE_COUNT> and returns the result.
1118 1352
1119=item $ctx = $kernel->context 1353=item $ctx = $kernel->context
1120 1354
1121Calls C<clGetKernelInfo> with C<CL_KERNEL_CONTEXT> and returns the result(s). 1355Calls C<clGetKernelInfo> with C<CL_KERNEL_CONTEXT> and returns the result.
1122 1356
1123=item $program = $kernel->program 1357=item $program = $kernel->program
1124 1358
1125Calls C<clGetKernelInfo> with C<CL_KERNEL_PROGRAM> and returns the result(s). 1359Calls C<clGetKernelInfo> with C<CL_KERNEL_PROGRAM> and returns the result.
1126 1360
1127=for gengetinfo end kernel 1361=for gengetinfo end kernel
1128 1362
1129=item $packed_value = $kernel->work_group_info ($device, $name) 1363=item $packed_value = $kernel->work_group_info ($device, $name)
1130 1364
… …
1137 1371
1138=for gengetinfo begin kernel_work_group 1372=for gengetinfo begin kernel_work_group
1139 1373
1140=item $int = $kernel->work_group_size ($device) 1374=item $int = $kernel->work_group_size ($device)
1141 1375
1142Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_WORK_GROUP_SIZE> and returns the result(s). 1376Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_WORK_GROUP_SIZE> and returns the result.
1143 1377
1144=item @ints = $kernel->compile_work_group_size ($device) 1378=item @ints = $kernel->compile_work_group_size ($device)
1145 1379
1146Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_COMPILE_WORK_GROUP_SIZE> and returns the result(s). 1380Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_COMPILE_WORK_GROUP_SIZE> and returns the result.
1147 1381
1148=item $ulong = $kernel->local_mem_size ($device) 1382=item $ulong = $kernel->local_mem_size ($device)
1149 1383
1150Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_LOCAL_MEM_SIZE> and returns the result(s). 1384Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_LOCAL_MEM_SIZE> and returns the result.
1151 1385
1152=item $int = $kernel->preferred_work_group_size_multiple ($device) 1386=item $int = $kernel->preferred_work_group_size_multiple ($device)
1153 1387
1154Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE> and returns the result(s). 1388Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE> and returns the result.
1155 1389
1156=item $ulong = $kernel->private_mem_size ($device) 1390=item $ulong = $kernel->private_mem_size ($device)
1157 1391
1158Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PRIVATE_MEM_SIZE> and returns the result(s). 1392Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PRIVATE_MEM_SIZE> and returns the result.
1159 1393
1160=for gengetinfo end kernel_work_group 1394=for gengetinfo end kernel_work_group
1161 1395
1162=item $kernel->set_TYPE ($index, $value) 1396=item $kernel->set_TYPE ($index, $value)
1163 1397
1164This is a family of methods to set the kernel argument with the number C<$index> to the give C<$value>. 1398This is a family of methods to set the kernel argument with the number C<$index> to the give C<$value>.
1165 1399
1166TYPE is one of C<char>, C<uchar>, C<short>, C<ushort>, C<int>, C<uint>, 1400TYPE is one of C<char>, C<uchar>, C<short>, C<ushort>, C<int>, C<uint>,
1167C<long>, C<ulong>, C<half>, C<float>, C<double>, C<memory>, C<buffer>, 1401C<long>, C<ulong>, C<half>, C<float>, C<double>, C<memory>, C<buffer>,
1168C<image2d>, C<image3d>, C<sampler> or C<event>. 1402C<image2d>, C<image3d>, C<sampler>, C<local> or C<event>.
1169 1403
1170Chars and integers (including the half type) are specified as integers, 1404Chars and integers (including the half type) are specified as integers,
1171float and double as floating point values, memory/buffer/image2d/image3d 1405float and double as floating point values, memory/buffer/image2d/image3d
1172must be an object of that type or C<undef>, and sampler and event must be 1406must be an object of that type or C<undef>, local-memory arguments are
1173objects of that type. 1407set by specifying the size, and sampler and event must be objects of that
1408type.
1174 1409
1175L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetKernelArg.html> 1410L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetKernelArg.html>
1176 1411
1177=back 1412=back
1178 1413
… …
1197 1432
1198=for gengetinfo begin event 1433=for gengetinfo begin event
1199 1434
1200=item $queue = $event->command_queue 1435=item $queue = $event->command_queue
1201 1436
1202Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_QUEUE> and returns the result(s). 1437Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_QUEUE> and returns the result.
1203 1438
1204=item $command_type = $event->command_type 1439=item $command_type = $event->command_type
1205 1440
1206Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_TYPE> and returns the result(s). 1441Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_TYPE> and returns the result.
1207 1442
1208=item $uint = $event->reference_count 1443=item $uint = $event->reference_count
1209 1444
1210Calls C<clGetEventInfo> with C<CL_EVENT_REFERENCE_COUNT> and returns the result(s). 1445Calls C<clGetEventInfo> with C<CL_EVENT_REFERENCE_COUNT> and returns the result.
1211 1446
1212=item $uint = $event->command_execution_status 1447=item $uint = $event->command_execution_status
1213 1448
1214Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_EXECUTION_STATUS> and returns the result(s). 1449Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_EXECUTION_STATUS> and returns the result.
1215 1450
1216=item $ctx = $event->context 1451=item $ctx = $event->context
1217 1452
1218Calls C<clGetEventInfo> with C<CL_EVENT_CONTEXT> and returns the result(s). 1453Calls C<clGetEventInfo> with C<CL_EVENT_CONTEXT> and returns the result.
1219 1454
1220=for gengetinfo end event 1455=for gengetinfo end event
1221 1456
1222=item $packed_value = $ev->profiling_info ($name) 1457=item $packed_value = $ev->profiling_info ($name)
1223 1458
… …
1230 1465
1231=for gengetinfo begin profiling 1466=for gengetinfo begin profiling
1232 1467
1233=item $ulong = $event->profiling_command_queued 1468=item $ulong = $event->profiling_command_queued
1234 1469
1235Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_QUEUED> and returns the result(s). 1470Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_QUEUED> and returns the result.
1236 1471
1237=item $ulong = $event->profiling_command_submit 1472=item $ulong = $event->profiling_command_submit
1238 1473
1239Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_SUBMIT> and returns the result(s). 1474Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_SUBMIT> and returns the result.
1240 1475
1241=item $ulong = $event->profiling_command_start 1476=item $ulong = $event->profiling_command_start
1242 1477
1243Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_START> and returns the result(s). 1478Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_START> and returns the result.
1244 1479
1245=item $ulong = $event->profiling_command_end 1480=item $ulong = $event->profiling_command_end
1246 1481
1247Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_END> and returns the result(s). 1482Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_END> and returns the result.
1248 1483
1249=for gengetinfo end profiling 1484=for gengetinfo end profiling
1250 1485
1251=back 1486=back
1252 1487
… …
1267package OpenCL; 1502package OpenCL;
1268 1503
1269use common::sense; 1504use common::sense;
1270 1505
1271BEGIN { 1506BEGIN {
1272 our $VERSION = '0.55'; 1507 our $VERSION = '0.96';
1273 1508
1274 require XSLoader; 1509 require XSLoader;
1275 XSLoader::load (__PACKAGE__, $VERSION); 1510 XSLoader::load (__PACKAGE__, $VERSION);
1276 1511
1277 @OpenCL::Buffer::ISA = 1512 @OpenCL::Buffer::ISA =
1278 @OpenCL::Image::ISA = OpenCL::Memory::; 1513 @OpenCL::Image::ISA = OpenCL::Memory::;
1279 1514
1515 @OpenCL::BufferObj::ISA = OpenCL::Buffer::;
1516
1280 @OpenCL::Image2D::ISA = 1517 @OpenCL::Image2D::ISA =
1518 @OpenCL::Image3D::ISA =
1519 @OpenCL::Image2DArray::ISA =
1520 @OpenCL::Image1D::ISA =
1521 @OpenCL::Image1DArray::ISA =
1281 @OpenCL::Image3D::ISA = OpenCL::Image::; 1522 @OpenCL::Image1DBuffer::ISA = OpenCL::Image::;
1282 1523
1283 @OpenCL::UserEvent::ISA = OpenCL::Event::; 1524 @OpenCL::UserEvent::ISA = OpenCL::Event::;
1284} 1525}
1285 1526
12861; 15271;
1287 1528
1288=head1 AUTHOR 1529=head1 AUTHOR

Diff Legend

– Removed lines
+ Added lines
< Changed lines
> Changed lines