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

Comparing OpenCL/OpenCL.pm (file contents):
Revision 1.18 by root, Thu Nov 17 06:22:29 2011 UTC vs.
Revision 1.34 by root, Thu Apr 19 13:06:55 2012 UTC

27OpenCL::Program objects, which store source code and, after building for a 27OpenCL::Program objects, which store source code and, after building for a
28specific device ("compiling and linking"), also binary programs. For each 28specific device ("compiling and linking"), also binary programs. For each
29kernel function in a program you can then create an OpenCL::Kernel object 29kernel function in a program you can then create an OpenCL::Kernel object
30which represents basically a function call with argument values. 30which represents basically a function call with argument values.
31 31
32OpenCL::Memory objects of various flavours: OpenCL::Buffers objects (flat 32OpenCL::Memory objects of various flavours: OpenCL::Buffer objects (flat
33memory areas, think arrays or structs) and OpenCL::Image objects (think 2d 33memory areas, think arrays or structs) and OpenCL::Image objects (think 2d
34or 3d array) for bulk data and input and output for kernels. 34or 3d array) for bulk data and input and output for kernels.
35 35
36OpenCL::Sampler objects, which are kind of like texture filter modes in 36OpenCL::Sampler objects, which are kind of like texture filter modes in
37OpenGL. 37OpenGL.
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); 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.
226 226
227=item * Object lifetime managament is automatic - there is no need 227=item * Object lifetime managament is automatic - there is no need
228to free objects explicitly (C<clReleaseXXX>), the release function 228to free objects explicitly (C<clReleaseXXX>), the release function
229is called automatically once all Perl references to it go away. 229is called automatically once all Perl references to it go away.
230 230
231=item * OpenCL uses CamelCase for function names (C<clGetPlatformInfo>), 231=item * OpenCL uses CamelCase for function names
232(e.g. C<clGetPlatformIDs>, C<clGetPlatformInfo>), while this module
232while this module uses underscores as word separator and often leaves out 233uses underscores as word separator and often leaves out prefixes
233prefixes (C<< $platform->info >>). 234(C<OpenCL::platforms>, C<< $platform->info >>).
234 235
235=item * OpenCL often specifies fixed vector function arguments as short 236=item * OpenCL often specifies fixed vector function arguments as short
236arrays (C<$origin[3]>), while this module explicitly expects the 237arrays (C<size_t origin[3]>), while this module explicitly expects the
237components as separate arguments- 238components as separate arguments (C<$orig_x, $orig_y, $orig_z>) in
239function calls.
238 240
239=item * Structures are often specified with their components, and returned 241=item * Structures are often specified by flattening out their components
240as arrayrefs. 242as with short vectors, and returned as arrayrefs.
241
242=item * Where possible, one of the pitch values is calculated from the
243perl scalar length and need not be specified.
244 243
245=item * When enqueuing commands, the wait list is specified by adding 244=item * When enqueuing commands, the wait list is specified by adding
246extra arguments to the function - anywhere a C<$wait_events...> argument 245extra arguments to the function - anywhere a C<$wait_events...> argument
247is documented this can be any number of event objects. 246is documented this can be any number of event objects.
248 247
287 286
288Comverts an error value into a human readable string. 287Comverts an error value into a human readable string.
289 288
290=item $str = OpenCL::enum2str $enum 289=item $str = OpenCL::enum2str $enum
291 290
292Converts most enum values (inof parameter names, image format constants, 291Converts most enum values (of parameter names, image format constants,
293object types, addressing and filter modes, command types etc.) into a 292object types, addressing and filter modes, command types etc.) into a
294human readbale string. When confronted with some random integer it can be 293human readable string. When confronted with some random integer it can be
295very helpful to pass it through this function to maybe get some readable 294very helpful to pass it through this function to maybe get some readable
296string out of it. 295string out of it.
297 296
298=item @platforms = OpenCL::platforms 297=item @platforms = OpenCL::platforms
299 298
317 316
318=head2 THE OpenCL::Platform CLASS 317=head2 THE OpenCL::Platform CLASS
319 318
320=over 4 319=over 4
321 320
322=item $packed_value = $platform->info ($name)
323
324Calls C<clGetPlatformInfo> and returns the packed, raw value - for
325strings, this will be the string, for other values you probably need to
326use the correct C<unpack>. This might get improved in the future. Hopefully.
327
328L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformInfo.html>
329
330=item @devices = $platform->devices ($type = OpenCL::DEVICE_TYPE_ALL) 321=item @devices = $platform->devices ($type = OpenCL::DEVICE_TYPE_ALL)
331 322
332Returns a list of matching OpenCL::Device objects. 323Returns a list of matching OpenCL::Device objects.
333 324
334=item $ctx = $platform->context_from_type ($properties, $type = OpenCL::DEVICE_TYPE_DEFAULT, $notify = undef) 325=item $ctx = $platform->context_from_type ($properties, $type = OpenCL::DEVICE_TYPE_DEFAULT, $notify = undef)
335 326
336Tries to create a context. Never worked for me, and you need devices explitly anyway. 327Tries to create a context. Never worked for me, and you need devices explicitly anyway.
337 328
338L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html> 329L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>
339 330
340=item $ctx = $device->context ($properties = undef, @$devices, $notify = undef) 331=item $ctx = $platform->context ($properties = undef, @$devices, $notify = undef)
341 332
342Create a new OpenCL::Context object using the given device object(s)- a 333Create a new OpenCL::Context object using the given device object(s)- a
343CL_CONTEXT_PLATFORM property is supplied automatically. 334CL_CONTEXT_PLATFORM property is supplied automatically.
344 335
345L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html> 336L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>
346 337
338=item $packed_value = $platform->info ($name)
339
340Calls C<clGetPlatformInfo> and returns the packed, raw value - for
341strings, this will be the string (possibly including terminating \0), for
342other values you probably need to use the correct C<unpack>.
343
344It's best to avoid this method and use one of the following convenience
345wrappers.
346
347L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformInfo.html>
348
349=for gengetinfo begin platform
350
351=item $string = $platform->profile
352
353Calls C<clGetPlatformInfo> with C<CL_PLATFORM_PROFILE> and returns the result.
354
355=item $string = $platform->version
356
357Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VERSION> and returns the result.
358
359=item $string = $platform->name
360
361Calls C<clGetPlatformInfo> with C<CL_PLATFORM_NAME> and returns the result.
362
363=item $string = $platform->vendor
364
365Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VENDOR> and returns the result.
366
367=item $string = $platform->extensions
368
369Calls C<clGetPlatformInfo> with C<CL_PLATFORM_EXTENSIONS> and returns the result.
370
371=for gengetinfo end platform
372
347=back 373=back
348 374
349=head2 THE OpenCL::Device CLASS 375=head2 THE OpenCL::Device CLASS
350 376
351=over 4 377=over 4
354 380
355See C<< $platform->info >> for details. 381See C<< $platform->info >> for details.
356 382
357L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetDeviceInfo.html> 383L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetDeviceInfo.html>
358 384
385=for gengetinfo begin device
386
387=item $device_type = $device->type
388
389Calls C<clGetDeviceInfo> with C<CL_DEVICE_TYPE> and returns the result.
390
391=item $uint = $device->vendor_id
392
393Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR_ID> and returns the result.
394
395=item $uint = $device->max_compute_units
396
397Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_COMPUTE_UNITS> and returns the result.
398
399=item $uint = $device->max_work_item_dimensions
400
401Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS> and returns the result.
402
403=item $int = $device->max_work_group_size
404
405Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_GROUP_SIZE> and returns the result.
406
407=item @ints = $device->max_work_item_sizes
408
409Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_SIZES> and returns the result.
410
411=item $uint = $device->preferred_vector_width_char
412
413Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR> and returns the result.
414
415=item $uint = $device->preferred_vector_width_short
416
417Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT> and returns the result.
418
419=item $uint = $device->preferred_vector_width_int
420
421Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT> and returns the result.
422
423=item $uint = $device->preferred_vector_width_long
424
425Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG> and returns the result.
426
427=item $uint = $device->preferred_vector_width_float
428
429Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT> and returns the result.
430
431=item $uint = $device->preferred_vector_width_double
432
433Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE> and returns the result.
434
435=item $uint = $device->max_clock_frequency
436
437Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CLOCK_FREQUENCY> and returns the result.
438
439=item $bitfield = $device->address_bits
440
441Calls C<clGetDeviceInfo> with C<CL_DEVICE_ADDRESS_BITS> and returns the result.
442
443=item $uint = $device->max_read_image_args
444
445Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_READ_IMAGE_ARGS> and returns the result.
446
447=item $uint = $device->max_write_image_args
448
449Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WRITE_IMAGE_ARGS> and returns the result.
450
451=item $ulong = $device->max_mem_alloc_size
452
453Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_MEM_ALLOC_SIZE> and returns the result.
454
455=item $int = $device->image2d_max_width
456
457Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_WIDTH> and returns the result.
458
459=item $int = $device->image2d_max_height
460
461Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_HEIGHT> and returns the result.
462
463=item $int = $device->image3d_max_width
464
465Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_WIDTH> and returns the result.
466
467=item $int = $device->image3d_max_height
468
469Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_HEIGHT> and returns the result.
470
471=item $int = $device->image3d_max_depth
472
473Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_DEPTH> and returns the result.
474
475=item $uint = $device->image_support
476
477Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE_SUPPORT> and returns the result.
478
479=item $int = $device->max_parameter_size
480
481Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_PARAMETER_SIZE> and returns the result.
482
483=item $uint = $device->max_samplers
484
485Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_SAMPLERS> and returns the result.
486
487=item $uint = $device->mem_base_addr_align
488
489Calls C<clGetDeviceInfo> with C<CL_DEVICE_MEM_BASE_ADDR_ALIGN> and returns the result.
490
491=item $uint = $device->min_data_type_align_size
492
493Calls C<clGetDeviceInfo> with C<CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE> and returns the result.
494
495=item $device_fp_config = $device->single_fp_config
496
497Calls C<clGetDeviceInfo> with C<CL_DEVICE_SINGLE_FP_CONFIG> and returns the result.
498
499=item $device_mem_cache_type = $device->global_mem_cache_type
500
501Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_TYPE> and returns the result.
502
503=item $uint = $device->global_mem_cacheline_size
504
505Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE> and returns the result.
506
507=item $ulong = $device->global_mem_cache_size
508
509Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_SIZE> and returns the result.
510
511=item $ulong = $device->global_mem_size
512
513Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_SIZE> and returns the result.
514
515=item $ulong = $device->max_constant_buffer_size
516
517Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE> and returns the result.
518
519=item $uint = $device->max_constant_args
520
521Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_ARGS> and returns the result.
522
523=item $device_local_mem_type = $device->local_mem_type
524
525Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_TYPE> and returns the result.
526
527=item $ulong = $device->local_mem_size
528
529Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_SIZE> and returns the result.
530
531=item $boolean = $device->error_correction_support
532
533Calls C<clGetDeviceInfo> with C<CL_DEVICE_ERROR_CORRECTION_SUPPORT> and returns the result.
534
535=item $int = $device->profiling_timer_resolution
536
537Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILING_TIMER_RESOLUTION> and returns the result.
538
539=item $boolean = $device->endian_little
540
541Calls C<clGetDeviceInfo> with C<CL_DEVICE_ENDIAN_LITTLE> and returns the result.
542
543=item $boolean = $device->available
544
545Calls C<clGetDeviceInfo> with C<CL_DEVICE_AVAILABLE> and returns the result.
546
547=item $boolean = $device->compiler_available
548
549Calls C<clGetDeviceInfo> with C<CL_DEVICE_COMPILER_AVAILABLE> and returns the result.
550
551=item $device_exec_capabilities = $device->execution_capabilities
552
553Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXECUTION_CAPABILITIES> and returns the result.
554
555=item $command_queue_properties = $device->properties
556
557Calls C<clGetDeviceInfo> with C<CL_DEVICE_QUEUE_PROPERTIES> and returns the result.
558
559=item $ = $device->platform
560
561Calls C<clGetDeviceInfo> with C<CL_DEVICE_PLATFORM> and returns the result.
562
563=item $string = $device->name
564
565Calls C<clGetDeviceInfo> with C<CL_DEVICE_NAME> and returns the result.
566
567=item $string = $device->vendor
568
569Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR> and returns the result.
570
571=item $string = $device->driver_version
572
573Calls C<clGetDeviceInfo> with C<CL_DRIVER_VERSION> and returns the result.
574
575=item $string = $device->profile
576
577Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILE> and returns the result.
578
579=item $string = $device->version
580
581Calls C<clGetDeviceInfo> with C<CL_DEVICE_VERSION> and returns the result.
582
583=item $string = $device->extensions
584
585Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXTENSIONS> and returns the result.
586
587=item $uint = $device->preferred_vector_width_half
588
589Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF> and returns the result.
590
591=item $uint = $device->native_vector_width_char
592
593Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR> and returns the result.
594
595=item $uint = $device->native_vector_width_short
596
597Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT> and returns the result.
598
599=item $uint = $device->native_vector_width_int
600
601Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_INT> and returns the result.
602
603=item $uint = $device->native_vector_width_long
604
605Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG> and returns the result.
606
607=item $uint = $device->native_vector_width_float
608
609Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT> and returns the result.
610
611=item $uint = $device->native_vector_width_double
612
613Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE> and returns the result.
614
615=item $uint = $device->native_vector_width_half
616
617Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF> and returns the result.
618
619=item $device_fp_config = $device->double_fp_config
620
621Calls C<clGetDeviceInfo> with C<CL_DEVICE_DOUBLE_FP_CONFIG> and returns the result.
622
623=item $device_fp_config = $device->half_fp_config
624
625Calls C<clGetDeviceInfo> with C<CL_DEVICE_HALF_FP_CONFIG> and returns the result.
626
627=item $boolean = $device->host_unified_memory
628
629Calls C<clGetDeviceInfo> with C<CL_DEVICE_HOST_UNIFIED_MEMORY> and returns the result.
630
631=item $device = $device->parent_device_ext
632
633Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARENT_DEVICE_EXT> and returns the result.
634
635=item @device_partition_property_exts = $device->partition_types_ext
636
637Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_TYPES_EXT> and returns the result.
638
639=item @device_partition_property_exts = $device->affinity_domains_ext
640
641Calls C<clGetDeviceInfo> with C<CL_DEVICE_AFFINITY_DOMAINS_EXT> and returns the result.
642
643=item $uint = $device->reference_count_ext
644
645Calls C<clGetDeviceInfo> with C<CL_DEVICE_REFERENCE_COUNT_EXT > and returns the result.
646
647=item @device_partition_property_exts = $device->partition_style_ext
648
649Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_STYLE_EXT> and returns the result.
650
651=for gengetinfo end device
652
359=back 653=back
360 654
361=head2 THE OpenCL::Context CLASS 655=head2 THE OpenCL::Context CLASS
362 656
363=over 4 657=over 4
364 658
365=item $packed_value = $ctx->info ($name)
366
367See C<< $platform->info >> for details.
368
369L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetContextInfo.html>
370
371=item $queue = $ctx->queue ($device, $properties) 659=item $queue = $ctx->queue ($device, $properties)
372 660
373Create a new OpenCL::Queue object from the context and the given device. 661Create a new OpenCL::Queue object from the context and the given device.
374 662
375L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateCommandQueue.html> 663L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateCommandQueue.html>
380 668
381L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateUserEvent.html> 669L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateUserEvent.html>
382 670
383=item $buf = $ctx->buffer ($flags, $len) 671=item $buf = $ctx->buffer ($flags, $len)
384 672
385Creates a new OpenCL::Buffer object with the given flags and octet-size. 673Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object with the
674given flags and octet-size.
386 675
387L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateBuffer.html> 676L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateBuffer.html>
388 677
389=item $buf = $ctx->buffer_sv ($flags, $data) 678=item $buf = $ctx->buffer_sv ($flags, $data)
390 679
391Creates a new OpenCL::Buffer object and initialise it with the given data values. 680Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object and
681initialise it with the given data values.
392 682
393=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef) 683=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef)
394 684
395Creates a new OpenCL::Image2D object and optionally initialises it with the given data values. 685Creates a new OpenCL::Image2D object and optionally initialises it with
686the given data values.
396 687
397L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage2D.html> 688L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage2D.html>
398 689
399=item $img = $ctx->image3d ($flags, $channel_order, $channel_type, $width, $height, $depth, $row_pitch = 0, $slice_pitch = 0, $data = undef) 690=item $img = $ctx->image3d ($flags, $channel_order, $channel_type, $width, $height, $depth, $row_pitch = 0, $slice_pitch = 0, $data = undef)
400 691
401Creates a new OpenCL::Image3D object and optionally initialises it with the given data values. 692Creates a new OpenCL::Image3D object and optionally initialises it with
693the given data values.
402 694
403L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage3D.html> 695L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateImage3D.html>
696
697=item $buffer = $ctx->gl_buffer ($flags, $bufobj)
698
699Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object that refers to the given
700OpenGL buffer object.
701
702http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLBuffer.html
703
704=item $ctx->gl_texture2d ($flags, $target, $miplevel, $texture)
705
706Creates a new OpenCL::Image2D object that refers to the given OpenGL
7072D texture object.
708
709http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture2D.html
710
711=item $ctx->gl_texture3d ($flags, $target, $miplevel, $texture)
712
713Creates a new OpenCL::Image3D object that refers to the given OpenGL
7143D texture object.
715
716http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLTexture3D.html
717
718=item $ctx->gl_renderbuffer ($flags, $renderbuffer)
719
720Creates a new OpenCL::Image2D object that refers to the given OpenGL
721render buffer.
722
723http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLRenderbuffer.html
404 724
405=item @formats = $ctx->supported_image_formats ($flags, $image_type) 725=item @formats = $ctx->supported_image_formats ($flags, $image_type)
406 726
407Returns a list of matching image formats - each format is an arrayref with 727Returns a list of matching image formats - each format is an arrayref with
408two values, $channel_order and $channel_type, in it. 728two values, $channel_order and $channel_type, in it.
418=item $program = $ctx->program_with_source ($string) 738=item $program = $ctx->program_with_source ($string)
419 739
420Creates a new OpenCL::Program object from the given source code. 740Creates a new OpenCL::Program object from the given source code.
421 741
422L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateProgramWithSource.html> 742L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateProgramWithSource.html>
743
744=item $packed_value = $ctx->info ($name)
745
746See C<< $platform->info >> for details.
747
748L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetContextInfo.html>
749
750=for gengetinfo begin context
751
752=item $uint = $context->reference_count
753
754Calls C<clGetContextInfo> with C<CL_CONTEXT_REFERENCE_COUNT> and returns the result.
755
756=item @devices = $context->devices
757
758Calls C<clGetContextInfo> with C<CL_CONTEXT_DEVICES> and returns the result.
759
760=item @property_ints = $context->properties
761
762Calls C<clGetContextInfo> with C<CL_CONTEXT_PROPERTIES> and returns the result.
763
764=item $uint = $context->num_devices
765
766Calls C<clGetContextInfo> with C<CL_CONTEXT_NUM_DEVICES> and returns the result.
767
768=for gengetinfo end context
423 769
424=back 770=back
425 771
426=head2 THE OpenCL::Queue CLASS 772=head2 THE OpenCL::Queue CLASS
427 773
441cases (i.e. you use only one queue) it's not necessary to wait for or 787cases (i.e. you use only one queue) it's not necessary to wait for or
442create event objects. 788create event objects.
443 789
444=over 4 790=over 4
445 791
446=item $packed_value = $ctx->info ($name)
447
448See C<< $platform->info >> for details.
449
450L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetCommandQueueInfo.html>
451
452=item $ev = $queue->enqueue_read_buffer ($buffer, $blocking, $offset, $len, $data, $wait_events...) 792=item $ev = $queue->enqueue_read_buffer ($buffer, $blocking, $offset, $len, $data, $wait_events...)
453 793
454Reads data from buffer into the given string. 794Reads data from buffer into the given string.
455 795
456L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadBuffer.html> 796L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadBuffer.html>
463 803
464=item $ev = $queue->enqueue_copy_buffer ($src, $dst, $src_offset, $dst_offset, $len, $wait_events...) 804=item $ev = $queue->enqueue_copy_buffer ($src, $dst, $src_offset, $dst_offset, $len, $wait_events...)
465 805
466L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBuffer.html> 806L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBuffer.html>
467 807
808=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...)
809
810http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadBufferRect.html
811
812=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...)
813
814http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteBufferRect.html
815
468=item $ev = $queue->enqueue_read_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...) 816=item $ev = $queue->enqueue_read_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...)
469 817
818L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferRect.html>
819
820=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...)
821
470L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadImage.html> 822L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadImage.html>
471 823
472=item $ev = $queue->enqueue_write_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...) 824=item $ev = $queue->enqueue_write_image ($src, $blocking, $x, $y, $z, $width, $height, $depth, $row_pitch, $slice_pitch, $data, $wait_events...)
473 825
474L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteImage.html> 826L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteImage.html>
475 827
828=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...)
829
830L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImage.html>
831
832=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...)
833
834L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImageToBuffer.html>
835
476=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...) 836=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...)
477 837
478Yeah. 838Yeah.
479 839
480L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferRect.html>
481
482=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...)
483
484L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferToImage.html>. 840L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBufferToImage.html>.
485
486=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...)
487
488L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImage.html>
489
490=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...)
491
492L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyImageToBuffer.html>
493 841
494=item $ev = $queue->enqueue_task ($kernel, $wait_events...) 842=item $ev = $queue->enqueue_task ($kernel, $wait_events...)
495 843
496L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueTask.html> 844L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueTask.html>
497 845
531 879
532=item $queue->finish 880=item $queue->finish
533 881
534L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFinish.html> 882L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clFinish.html>
535 883
884=item $packed_value = $queue->info ($name)
885
886See C<< $platform->info >> for details.
887
888L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetCommandQueueInfo.html>
889
890=for gengetinfo begin command_queue
891
892=item $ctx = $command_queue->context
893
894Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_CONTEXT> and returns the result.
895
896=item $device = $command_queue->device
897
898Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_DEVICE> and returns the result.
899
900=item $uint = $command_queue->reference_count
901
902Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_REFERENCE_COUNT> and returns the result.
903
904=item $command_queue_properties = $command_queue->properties
905
906Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_PROPERTIES> and returns the result.
907
908=for gengetinfo end command_queue
909
536=back 910=back
537 911
538=head2 THE OpenCL::Memory CLASS 912=head2 THE OpenCL::Memory CLASS
539 913
540This the superclass of all memory objects - OpenCL::Buffer, OpenCL::Image, 914This the superclass of all memory objects - OpenCL::Buffer, OpenCL::Image,
541OpenCL::Image2D and OpenCL::Image3D. The subclasses of this class 915OpenCL::Image2D and OpenCL::Image3D.
542currently only exist to allow type-checking.
543 916
544=over 4 917=over 4
545 918
546=item $packed_value = $memory->info ($name) 919=item $packed_value = $memory->info ($name)
547 920
548See C<< $platform->info >> for details. 921See C<< $platform->info >> for details.
549 922
550L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetMemObjectInfo.html> 923L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetMemObjectInfo.html>
551 924
925=for gengetinfo begin mem
926
927=item $mem_object_type = $mem->type
928
929Calls C<clGetMemObjectInfo> with C<CL_MEM_TYPE> and returns the result.
930
931=item $mem_flags = $mem->flags
932
933Calls C<clGetMemObjectInfo> with C<CL_MEM_FLAGS> and returns the result.
934
935=item $int = $mem->size
936
937Calls C<clGetMemObjectInfo> with C<CL_MEM_SIZE> and returns the result.
938
939=item $ptr_value = $mem->host_ptr
940
941Calls C<clGetMemObjectInfo> with C<CL_MEM_HOST_PTR> and returns the result.
942
943=item $uint = $mem->map_count
944
945Calls C<clGetMemObjectInfo> with C<CL_MEM_MAP_COUNT> and returns the result.
946
947=item $uint = $mem->reference_count
948
949Calls C<clGetMemObjectInfo> with C<CL_MEM_REFERENCE_COUNT> and returns the result.
950
951=item $ctx = $mem->context
952
953Calls C<clGetMemObjectInfo> with C<CL_MEM_CONTEXT> and returns the result.
954
955=item $mem = $mem->associated_memobject
956
957Calls C<clGetMemObjectInfo> with C<CL_MEM_ASSOCIATED_MEMOBJECT> and returns the result.
958
959=item $int = $mem->offset
960
961Calls C<clGetMemObjectInfo> with C<CL_MEM_OFFSET> and returns the result.
962
963=for gengetinfo end mem
964
965=item ($type, $name) = $mem->gl_object_info
966
967Returns the OpenGL object type (e.g. OpenCL::GL_OBJECT_TEXTURE2D) and the
968object "name" (e.g. the texture name) used to create this memory object.
969
970L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetGLObjectInfo.html>
971
552=back 972=back
553 973
974=head2 THE OpenCL::Buffer CLASS
975
976This is a subclass of OpenCL::Memory, and the superclass of
977OpenCL::BufferObj. Its purpose is simply to distinguish between buffers
978and sub-buffers.
979
980=head2 THE OpenCL::BufferObj CLASS
981
982This is a subclass of OpenCL::Buffer and thus OpenCL::Memory. It exists
983because one cna create sub buffers of OpenLC::BufferObj objects, but not
984sub buffers from these sub buffers.
985
986=over 4
987
988=item $subbuf = $buf_obj->sub_buffer_region ($flags, $origin, $size)
989
990Creates an OpenCL::Buffer objects from this buffer and returns it. The
991C<buffer_create_type> is assumed to be C<CL_BUFFER_CREATE_TYPE_REGION>.
992
993L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSubBuffer.html>
994
995=back
996
997=head2 THE OpenCL::Image CLASS
998
999This is the superclass of all image objects - OpenCL::Image2D and OpenCL::Image3D.
1000
1001=over 4
1002
1003=item $packed_value = $ev->image_info ($name)
1004
1005See C<< $platform->info >> for details.
1006
1007The reason this method is not called C<info> is that there already is an
1008C<< ->info >> method inherited from C<OpenCL::Memory>.
1009
1010L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetImageInfo.html>
1011
1012=for gengetinfo begin image
1013
1014=item $int = $image->element_size
1015
1016Calls C<clGetImageInfo> with C<CL_IMAGE_ELEMENT_SIZE> and returns the result.
1017
1018=item $int = $image->row_pitch
1019
1020Calls C<clGetImageInfo> with C<CL_IMAGE_ROW_PITCH> and returns the result.
1021
1022=item $int = $image->slice_pitch
1023
1024Calls C<clGetImageInfo> with C<CL_IMAGE_SLICE_PITCH> and returns the result.
1025
1026=item $int = $image->width
1027
1028Calls C<clGetImageInfo> with C<CL_IMAGE_WIDTH> and returns the result.
1029
1030=item $int = $image->height
1031
1032Calls C<clGetImageInfo> with C<CL_IMAGE_HEIGHT> and returns the result.
1033
1034=item $int = $image->depth
1035
1036Calls C<clGetImageInfo> with C<CL_IMAGE_DEPTH> and returns the result.
1037
1038=for gengetinfo end image
1039
1040=for gengetinfo begin gl_texture
1041
1042=item $GLenum = $gl_texture->target
1043
1044Calls C<clGetGlTextureInfo> with C<CL_GL_TEXTURE_TARGET> and returns the result.
1045
1046=item $GLint = $gl_texture->gl_mipmap_level
1047
1048Calls C<clGetGlTextureInfo> with C<CL_GL_MIPMAP_LEVEL> and returns the result.
1049
1050=for gengetinfo end gl_texture
1051
1052=back
1053
554=head2 THE OpenCL::Sampler CLASS 1054=head2 THE OpenCL::Sampler CLASS
555 1055
556=over 4 1056=over 4
557 1057
558=item $packed_value = $sampler->info ($name) 1058=item $packed_value = $sampler->info ($name)
559 1059
560See C<< $platform->info >> for details. 1060See C<< $platform->info >> for details.
561 1061
562L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetSamplerInfo.html> 1062L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetSamplerInfo.html>
563 1063
1064=for gengetinfo begin sampler
1065
1066=item $uint = $sampler->reference_count
1067
1068Calls C<clGetSamplerInfo> with C<CL_SAMPLER_REFERENCE_COUNT> and returns the result.
1069
1070=item $ctx = $sampler->context
1071
1072Calls C<clGetSamplerInfo> with C<CL_SAMPLER_CONTEXT> and returns the result.
1073
1074=item $addressing_mode = $sampler->normalized_coords
1075
1076Calls C<clGetSamplerInfo> with C<CL_SAMPLER_NORMALIZED_COORDS> and returns the result.
1077
1078=item $filter_mode = $sampler->addressing_mode
1079
1080Calls C<clGetSamplerInfo> with C<CL_SAMPLER_ADDRESSING_MODE> and returns the result.
1081
1082=item $boolean = $sampler->filter_mode
1083
1084Calls C<clGetSamplerInfo> with C<CL_SAMPLER_FILTER_MODE> and returns the result.
1085
1086=for gengetinfo end sampler
1087
564=back 1088=back
565 1089
566=head2 THE OpenCL::Program CLASS 1090=head2 THE OpenCL::Program CLASS
567 1091
568=over 4 1092=over 4
569
570=item $packed_value = $program->info ($name)
571
572See C<< $platform->info >> for details.
573
574L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetProgramInfo.html>
575 1093
576=item $program->build ($device, $options = "") 1094=item $program->build ($device, $options = "")
577 1095
578Tries to build the program with the givne options. 1096Tries to build the program with the givne options.
579 1097
591Creates an OpenCL::Kernel object out of the named C<__kernel> function in 1109Creates an OpenCL::Kernel object out of the named C<__kernel> function in
592the program. 1110the program.
593 1111
594L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateKernel.html> 1112L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateKernel.html>
595 1113
1114=for gengetinfo begin program_build
1115
1116=item $build_status = $program->build_status ($device)
1117
1118Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_STATUS> and returns the result.
1119
1120=item $string = $program->build_options ($device)
1121
1122Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_OPTIONS> and returns the result.
1123
1124=item $string = $program->build_log ($device)
1125
1126Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_LOG> and returns the result.
1127
1128=for gengetinfo end program_build
1129
1130=item $packed_value = $program->info ($name)
1131
1132See C<< $platform->info >> for details.
1133
1134L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetProgramInfo.html>
1135
1136=for gengetinfo begin program
1137
1138=item $uint = $program->reference_count
1139
1140Calls C<clGetProgramInfo> with C<CL_PROGRAM_REFERENCE_COUNT> and returns the result.
1141
1142=item $ctx = $program->context
1143
1144Calls C<clGetProgramInfo> with C<CL_PROGRAM_CONTEXT> and returns the result.
1145
1146=item $uint = $program->num_devices
1147
1148Calls C<clGetProgramInfo> with C<CL_PROGRAM_NUM_DEVICES> and returns the result.
1149
1150=item @devices = $program->devices
1151
1152Calls C<clGetProgramInfo> with C<CL_PROGRAM_DEVICES> and returns the result.
1153
1154=item $string = $program->source
1155
1156Calls C<clGetProgramInfo> with C<CL_PROGRAM_SOURCE> and returns the result.
1157
1158=item @ints = $program->binary_sizes
1159
1160Calls C<clGetProgramInfo> with C<CL_PROGRAM_BINARY_SIZES> and returns the result.
1161
1162=for gengetinfo end program
1163
1164=item @blobs = $program->binaries
1165
1166Returns a string for the compiled binary for every device associated with
1167the program, empty strings indicate missing programs, and an empty result
1168means no program binaries are available.
1169
1170These "binaries" are often, in fact, informative low-level assembly
1171sources.
1172
1173L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetProgramInfo.html>
1174
596=back 1175=back
597 1176
598=head2 THE OpenCL::Kernel CLASS 1177=head2 THE OpenCL::Kernel CLASS
599 1178
600=over 4 1179=over 4
602=item $packed_value = $kernel->info ($name) 1181=item $packed_value = $kernel->info ($name)
603 1182
604See C<< $platform->info >> for details. 1183See C<< $platform->info >> for details.
605 1184
606L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetKernelInfo.html> 1185L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetKernelInfo.html>
1186
1187=for gengetinfo begin kernel
1188
1189=item $string = $kernel->function_name
1190
1191Calls C<clGetKernelInfo> with C<CL_KERNEL_FUNCTION_NAME> and returns the result.
1192
1193=item $uint = $kernel->num_args
1194
1195Calls C<clGetKernelInfo> with C<CL_KERNEL_NUM_ARGS> and returns the result.
1196
1197=item $uint = $kernel->reference_count
1198
1199Calls C<clGetKernelInfo> with C<CL_KERNEL_REFERENCE_COUNT> and returns the result.
1200
1201=item $ctx = $kernel->context
1202
1203Calls C<clGetKernelInfo> with C<CL_KERNEL_CONTEXT> and returns the result.
1204
1205=item $program = $kernel->program
1206
1207Calls C<clGetKernelInfo> with C<CL_KERNEL_PROGRAM> and returns the result.
1208
1209=for gengetinfo end kernel
1210
1211=item $packed_value = $kernel->work_group_info ($device, $name)
1212
1213See C<< $platform->info >> for details.
1214
1215The reason this method is not called C<info> is that there already is an
1216C<< ->info >> method.
1217
1218L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetKernelWorkGroupInfo.html>
1219
1220=for gengetinfo begin kernel_work_group
1221
1222=item $int = $kernel->work_group_size ($device)
1223
1224Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_WORK_GROUP_SIZE> and returns the result.
1225
1226=item @ints = $kernel->compile_work_group_size ($device)
1227
1228Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_COMPILE_WORK_GROUP_SIZE> and returns the result.
1229
1230=item $ulong = $kernel->local_mem_size ($device)
1231
1232Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_LOCAL_MEM_SIZE> and returns the result.
1233
1234=item $int = $kernel->preferred_work_group_size_multiple ($device)
1235
1236Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE> and returns the result.
1237
1238=item $ulong = $kernel->private_mem_size ($device)
1239
1240Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PRIVATE_MEM_SIZE> and returns the result.
1241
1242=for gengetinfo end kernel_work_group
607 1243
608=item $kernel->set_TYPE ($index, $value) 1244=item $kernel->set_TYPE ($index, $value)
609 1245
610This is a family of methods to set the kernel argument with the number C<$index> to the give C<$value>. 1246This is a family of methods to set the kernel argument with the number C<$index> to the give C<$value>.
611 1247
627This is the superclass for all event objects (including OpenCL::UserEvent 1263This is the superclass for all event objects (including OpenCL::UserEvent
628objects). 1264objects).
629 1265
630=over 4 1266=over 4
631 1267
1268=item $ev->wait
1269
1270Waits for the event to complete.
1271
1272L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clWaitForEvents.html>
1273
632=item $packed_value = $ev->info ($name) 1274=item $packed_value = $ev->info ($name)
633 1275
634See C<< $platform->info >> for details. 1276See C<< $platform->info >> for details.
635 1277
636L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetEventInfo.html> 1278L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetEventInfo.html>
637 1279
638=item $ev->wait 1280=for gengetinfo begin event
639 1281
640Waits for the event to complete. 1282=item $queue = $event->command_queue
641 1283
1284Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_QUEUE> and returns the result.
1285
1286=item $command_type = $event->command_type
1287
1288Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_TYPE> and returns the result.
1289
1290=item $uint = $event->reference_count
1291
1292Calls C<clGetEventInfo> with C<CL_EVENT_REFERENCE_COUNT> and returns the result.
1293
1294=item $uint = $event->command_execution_status
1295
1296Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_EXECUTION_STATUS> and returns the result.
1297
1298=item $ctx = $event->context
1299
1300Calls C<clGetEventInfo> with C<CL_EVENT_CONTEXT> and returns the result.
1301
1302=for gengetinfo end event
1303
1304=item $packed_value = $ev->profiling_info ($name)
1305
1306See C<< $platform->info >> for details.
1307
1308The reason this method is not called C<info> is that there already is an
1309C<< ->info >> method.
1310
642L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clWaitForEvents.html> 1311L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetProfilingInfo.html>
1312
1313=for gengetinfo begin profiling
1314
1315=item $ulong = $event->profiling_command_queued
1316
1317Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_QUEUED> and returns the result.
1318
1319=item $ulong = $event->profiling_command_submit
1320
1321Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_SUBMIT> and returns the result.
1322
1323=item $ulong = $event->profiling_command_start
1324
1325Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_START> and returns the result.
1326
1327=item $ulong = $event->profiling_command_end
1328
1329Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_END> and returns the result.
1330
1331=for gengetinfo end profiling
643 1332
644=back 1333=back
645 1334
646=head2 THE OpenCL::UserEvent CLASS 1335=head2 THE OpenCL::UserEvent CLASS
647 1336
660package OpenCL; 1349package OpenCL;
661 1350
662use common::sense; 1351use common::sense;
663 1352
664BEGIN { 1353BEGIN {
665 our $VERSION = '0.15'; 1354 our $VERSION = '0.92';
666 1355
667 require XSLoader; 1356 require XSLoader;
668 XSLoader::load (__PACKAGE__, $VERSION); 1357 XSLoader::load (__PACKAGE__, $VERSION);
669 1358
670 @OpenCL::Buffer::ISA = 1359 @OpenCL::Buffer::ISA =
671 @OpenCL::Image::ISA = OpenCL::Memory::; 1360 @OpenCL::Image::ISA = OpenCL::Memory::;
672 1361
1362 @OpenCL::BufferObj::ISA = OpenCL::Buffer::;
1363
673 @OpenCL::Image2D::ISA = 1364 @OpenCL::Image2D::ISA =
674 @OpenCL::Image3D::ISA = OpenCL::Image::; 1365 @OpenCL::Image3D::ISA = OpenCL::Image::;
675 1366
676 @OpenCL::UserEvent::ISA = OpenCL::Event::; 1367 @OpenCL::UserEvent::ISA = OpenCL::Event::;
677} 1368}
678 1369
6791; 13701;
680 1371
681=head1 AUTHOR 1372=head1 AUTHOR

Diff Legend

Removed lines
+ Added lines
< Changed lines
> Changed lines