[ViewVC] Diff of: cvs/OpenCL/OpenCL.pm

Comparing OpenCL/OpenCL.pm (file contents):
Revision 1.67 by root, Tue May 1 22:04:56 2012 UTC vs.
Revision 1.80 by root, Sat May 5 13:55:59 2012 UTC

…		…
28	specific device ("compiling and linking"), also binary programs. For each	28	specific device ("compiling and linking"), also binary programs. For each
29	kernel function in a program you can then create an OpenCL::Kernel object	29	kernel function in a program you can then create an OpenCL::Kernel object
30	which represents basically a function call with argument values.	30	which represents basically a function call with argument values.
31		31
32	OpenCL::Memory objects of various flavours: OpenCL::Buffer objects (flat	32	OpenCL::Memory objects of various flavours: OpenCL::Buffer objects (flat
33	memory areas, think arrays or structs) and OpenCL::Image objects (think 2d	33	memory areas, think arrays or structs) and OpenCL::Image objects (think 2D
34	or 3d array) for bulk data and input and output for kernels.	34	or 3D array) for bulk data and input and output for kernels.
35		35
36	OpenCL::Sampler objects, which are kind of like texture filter modes in	36	OpenCL::Sampler objects, which are kind of like texture filter modes in
37	OpenGL.	37	OpenGL.
38		38
39	OpenCL::Queue objects - command queues, which allow you to submit memory	39	OpenCL::Queue objects - command queues, which allow you to submit memory
…		…
43		43
44	OpenCL::Event objects are used to signal when something is complete.	44	OpenCL::Event objects are used to signal when something is complete.
45		45
46	=head2 HELPFUL RESOURCES	46	=head2 HELPFUL RESOURCES
47		47
48	The OpenCL specs used to develop this module:	48	The OpenCL specs used to develop this module - download these and keept
		49	hema round, they are required reference material:
49		50
50	http://www.khronos.org/registry/cl/specs/opencl-1.1.pdf	51	http://www.khronos.org/registry/cl/specs/opencl-1.1.pdf
51	http://www.khronos.org/registry/cl/specs/opencl-1.2.pdf	52	http://www.khronos.org/registry/cl/specs/opencl-1.2.pdf
52	http://www.khronos.org/registry/cl/specs/opencl-1.2-extensions.pdf	53	http://www.khronos.org/registry/cl/specs/opencl-1.2-extensions.pdf
53		54
…		…
210		211
211	# wait for the last event to complete	212	# wait for the last event to complete
212	$ev->wait;	213	$ev->wait;
213		214
214	=head2 Use the OpenGL module to share a texture between OpenCL and OpenGL and draw some julia	215	=head2 Use the OpenGL module to share a texture between OpenCL and OpenGL and draw some julia
215	set tunnel effect.	216	set flight effect.
216		217
217	This is quite a long example to get you going - you can download it from	218	This is quite a long example to get you going - you can download it from
218	L<http://cvs.schmorp.de/OpenCL/examples/juliaflight>.	219	L<http://cvs.schmorp.de/OpenCL/examples/juliaflight>.
219		220
220	use OpenGL ":all";	221	use OpenGL ":all";
…		…
320	To use a texture, you would modify the above example by creating an	321	To use a texture, you would modify the above example by creating an
321	OpenCL::Image manually instead of deriving it from a texture:	322	OpenCL::Image manually instead of deriving it from a texture:
322		323
323	my $tex = $ctx->image2d (OpenCL::MEM_WRITE_ONLY, OpenCL::RGBA, OpenCL::UNORM_INT8, $S, $S);	324	my $tex = $ctx->image2d (OpenCL::MEM_WRITE_ONLY, OpenCL::RGBA, OpenCL::UNORM_INT8, $S, $S);
324		325
325	And in the darw loop, intead of acquire_gl_objects/release_gl_objects, you	326	And in the draw loop, intead of acquire_gl_objects/release_gl_objects, you
326	would read the image2d after the kernel has written it:	327	would read the image2d after the kernel has written it:
327		328
328	$queue->read_image ($tex, 0, 0, 0, 0, $S, $S, 1, 0, 0, my $data);	329	$queue->read_image ($tex, 0, 0, 0, 0, $S, $S, 1, 0, 0, my $data);
329		330
330	And then you would upload the pixel data to the texture (or use glDrawPixels):	331	And then you would upload the pixel data to the texture (or use glDrawPixels):
331		332
332	glTexSubImage2D_s GL_TEXTURE_2D, 0, 0, 0, $S, $S, GL_RGBA, GL_UNSIGNED_BYTE, $data;	333	glTexSubImage2D_s GL_TEXTURE_2D, 0, 0, 0, $S, $S, GL_RGBA, GL_UNSIGNED_BYTE, $data;
333		334
334	The fully modified example can be found at	335	The fully modified example can be found at
335	L<http://cvs.schmorp.de/OpenCL/examples/juliaflight-nosharing>.	336	L<http://cvs.schmorp.de/OpenCL/examples/juliaflight-nosharing>.
		337
		338	=head2 Julia sets look soooo 80ies.
		339
		340	Then colour them differently, e.g. using orbit traps! Replace the loop and
		341	colour calculation from the previous examples by this:
		342
		343	float2 dm = (float2)(1.f, 1.f);
		344
		345	for (int i = 0; i < 25; ++i)
		346	{
		347	z = (float2)(z.x * z.x - z.y * z.y, 2.f * z.x * z.y) + c;
		348	dm = fmin (dm, (float2)(fabs (dot (z, z) - 1.f), fabs (z.x - 1.f)));
		349	}
		350
		351	float3 colour = (float3)(dm.x * dm.y, dm.x * dm.y, dm.x);
		352
		353	Also try C<-10.f> instead of C<-1.f>.
336		354
337	=head1 DOCUMENTATION	355	=head1 DOCUMENTATION
338		356
339	=head2 BASIC CONVENTIONS	357	=head2 BASIC CONVENTIONS
340		358
…		…
370		388
371	=item * When enqueuing commands, if the enqueue method is called in void	389	=item * When enqueuing commands, if the enqueue method is called in void
372	context, no event is created. In all other contexts an event is returned	390	context, no event is created. In all other contexts an event is returned
373	by the method.	391	by the method.
374		392
375	=item * This module expects all functions to return C<CL_SUCCESS>. If any	393	=item * This module expects all functions to return C<OpenCL::SUCCESS>. If any
376	other status is returned the function will throw an exception, so you	394	other status is returned the function will throw an exception, so you
377	don't normally have to to any error checking.	395	don't normally have to to any error checking.
378		396
379	=back	397	=back
		398
		399	=head2 CONSTANTS
		400
		401	All C<CL_xxx> constants that this module supports are always available
		402	in the C<OpenCL> namespace as C<OpenCL::xxx> (i.e. without the C<CL_>
		403	prefix). Constants which are not defined in the heaer files used during
		404	compilation, or otherwise are not available, will have the value C<-1>.
		405
		406	=head2 OPENCL 1.1 VS. OPENCL 1.2
		407
		408	This module supports both OpenCL version 1.1 and 1.2, although the OpenCL
		409	1.2 interface hasn't been tested much for lack of availability of an
		410	actual implementation.
		411
		412	Every function or method in this manual page that interfaces to a
		413	particular OpenCL function has a link to the its C manual page.
		414
		415	If the link contains a F<1.1>, then this function is an OpenCL 1.1
		416	function. Most but not all also exist in OpenCL 1.2, and this module
		417	tries to emulate the missing ones for you, when told to do so at
		418	compiletime. You cna check whether a function was removed in OpenCL 1.2 by
		419	replacing the F<1.1> component in the URL by F<1.2>.
		420
		421	If the link contains a F<1.2>, then this is a OpenCL 1.2-only
		422	function. Even if the module was compiled with OpenCL 1.2 header files
		423	and has an 1.2 OpenCL library, calling such a function on a platform that
		424	doesn't implement 1.2 causes undefined behaviour, usually a crash (But
		425	this is not guaranteed).
		426
		427	You can find out whether this module was compiled to prefer 1.1
		428	functionality by ooking at C<OpenCL::PREFER_1_1> - if it is true, then
		429	1.1 functions generally are implemented using 1.1 OpenCL functions. If it
		430	is false, then 1.1 functions missing from 1.2 are emulated by calling 1.2
		431	fucntions.
		432
		433	This is a somewhat sorry state of affairs, but the Khronos group choose to
		434	make every release of OpenCL source and binary incompatible with previous
		435	releases.
380		436
381	=head2 PERL AND OPENCL TYPES	437	=head2 PERL AND OPENCL TYPES
382		438
383	This handy(?) table lists OpenCL types and their perl, PDL and pack/unpack	439	This handy(?) table lists OpenCL types and their perl, PDL and pack/unpack
384	format equivalents:	440	format equivalents:
…		…
416	OpenCL can generate a number of (potentially) asynchronous events, for	472	OpenCL can generate a number of (potentially) asynchronous events, for
417	example, after compiling a program, to signal a context-related error or,	473	example, after compiling a program, to signal a context-related error or,
418	perhaps most important, to signal completion of queued jobs (by setting	474	perhaps most important, to signal completion of queued jobs (by setting
419	callbacks on OpenCL::Event objects).	475	callbacks on OpenCL::Event objects).
420		476
		477	The OpenCL module converts all these callbacks into events - you can
		478	still register callbacks, but they are not executed when your OpenCL
		479	implementation calls the actual callback, but only later. Therefore, none
		480	of the limitations of OpenCL callbacks apply to the perl implementation:
		481	it is perfectly safe to make blocking operations from event callbacks, and
		482	enqueued operations don't need to be flushed.
		483
421	To facilitate this, this module maintains an event queue - each	484	To facilitate this, this module maintains an event queue - each
422	time an asynchronous event happens, it is queued, and perl will be	485	time an asynchronous event happens, it is queued, and perl will be
423	interrupted. This is implemented via the L<Async::Interrupt> module. In	486	interrupted. This is implemented via the L<Async::Interrupt> module. In
424	addition, this module has L<AnyEvent> support, so it can seamlessly	487	addition, this module has L<AnyEvent> support, so it can seamlessly
425	integrate itself into many event loops.	488	integrate itself into many event loops.
426		489
427	Since this module is a bit hard to understand, here are some case examples:	490	Since L<Async::Interrupt> is a bit hard to understand, here are some case examples:
428		491
429	=head3 Don't use callbacks.	492	=head3 Don't use callbacks.
430		493
431	When your program never uses any callbacks, then there will never be any	494	When your program never uses any callbacks, then there will never be any
432	notifications you need to take care of, and therefore no need to worry	495	notifications you need to take care of, and therefore no need to worry
…		…
529	use Async::Interrupt ();	592	use Async::Interrupt ();
530		593
531	our $POLL_FUNC; # set by XS	594	our $POLL_FUNC; # set by XS
532		595
533	BEGIN {	596	BEGIN {
534	our $VERSION = '0.98';	597	our $VERSION = '0.99';
535		598
536	require XSLoader;	599	require XSLoader;
537	XSLoader::load (__PACKAGE__, $VERSION);	600	XSLoader::load (__PACKAGE__, $VERSION);
538		601
539	@OpenCL::Platform::ISA =	602	@OpenCL::Platform::ISA =
…		…
544	@OpenCL::Sampler::ISA =	607	@OpenCL::Sampler::ISA =
545	@OpenCL::Program::ISA =	608	@OpenCL::Program::ISA =
546	@OpenCL::Kernel::ISA =	609	@OpenCL::Kernel::ISA =
547	@OpenCL::Event::ISA = OpenCL::Object::;	610	@OpenCL::Event::ISA = OpenCL::Object::;
548		611
		612	@OpenCL::SubDevice::ISA = OpenCL::Device::;
		613
549	@OpenCL::Buffer::ISA =	614	@OpenCL::Buffer::ISA =
550	@OpenCL::Image::ISA = OpenCL::Memory::;	615	@OpenCL::Image::ISA = OpenCL::Memory::;
551		616
552	@OpenCL::BufferObj::ISA = OpenCL::Buffer::;	617	@OpenCL::BufferObj::ISA = OpenCL::Buffer::;
553		618
…		…
593	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformIDs.html>	658	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformIDs.html>
594		659
595	=item $ctx = OpenCL::context_from_type $properties, $type = OpenCL::DEVICE_TYPE_DEFAULT, $callback->($err, $pvt) = $print_stderr	660	=item $ctx = OpenCL::context_from_type $properties, $type = OpenCL::DEVICE_TYPE_DEFAULT, $callback->($err, $pvt) = $print_stderr
596		661
597	Tries to create a context from a default device and platform type - never worked for me.	662	Tries to create a context from a default device and platform type - never worked for me.
		663	Consider using C<< $platform->context_from_type >> instead.
		664
		665	type: OpenCL::DEVICE_TYPE_DEFAULT, OpenCL::DEVICE_TYPE_CPU, OpenCL::DEVICE_TYPE_GPU,
		666	OpenCL::DEVICE_TYPE_ACCELERATOR, OpenCL::DEVICE_TYPE_CUSTOM, OpenCL::DEVICE_TYPE_ALL.
598		667
599	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>	668	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>
600		669
601	=item $ctx = OpenCL::context $properties, \@devices, $callback->($err, $pvt) = $print_stderr)	670	=item $ctx = OpenCL::context $properties, \@devices, $callback->($err, $pvt) = $print_stderr)
602		671
603	Create a new OpenCL::Context object using the given device object(s). This	672	Create a new OpenCL::Context object using the given device object(s).
604	function isn't implemented yet, use C<< $platform->context >> instead.	673	Consider using C<< $platform->context >> instead.
605		674
606	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>	675	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>
607		676
608	=item OpenCL::wait_for_events $wait_events...	677	=item OpenCL::wait_for_events $wait_events...
609		678
…		…
690	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>	759	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>
691		760
692	=item $ctx = $platform->context ($properties, \@devices, $callback->($err, $pvt) = $print_stderr)	761	=item $ctx = $platform->context ($properties, \@devices, $callback->($err, $pvt) = $print_stderr)
693		762
694	Create a new OpenCL::Context object using the given device object(s)- a	763	Create a new OpenCL::Context object using the given device object(s)- a
695	CL_CONTEXT_PLATFORM property is supplied automatically.	764	OpenCL::CONTEXT_PLATFORM property is supplied automatically.
696		765
697	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>	766	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>
698		767
699	=item $packed_value = $platform->info ($name)	768	=item $packed_value = $platform->info ($name)
700		769
…		…
716		785
717	=for gengetinfo begin platform	786	=for gengetinfo begin platform
718		787
719	=item $string = $platform->profile	788	=item $string = $platform->profile
720		789
721	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_PROFILE> and returns the result.	790	Calls C<clGetPlatformInfo> with C<OpenCL::PLATFORM_PROFILE> and returns the result.
722		791
723	=item $string = $platform->version	792	=item $string = $platform->version
724		793
725	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VERSION> and returns the result.	794	Calls C<clGetPlatformInfo> with C<OpenCL::PLATFORM_VERSION> and returns the result.
726		795
727	=item $string = $platform->name	796	=item $string = $platform->name
728		797
729	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_NAME> and returns the result.	798	Calls C<clGetPlatformInfo> with C<OpenCL::PLATFORM_NAME> and returns the result.
730		799
731	=item $string = $platform->vendor	800	=item $string = $platform->vendor
732		801
733	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VENDOR> and returns the result.	802	Calls C<clGetPlatformInfo> with C<OpenCL::PLATFORM_VENDOR> and returns the result.
734		803
735	=item $string = $platform->extensions	804	=item $string = $platform->extensions
736		805
737	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_EXTENSIONS> and returns the result.	806	Calls C<clGetPlatformInfo> with C<OpenCL::PLATFORM_EXTENSIONS> and returns the result.
738		807
739	=for gengetinfo end platform	808	=for gengetinfo end platform
740		809
741	=back	810	=back
742		811
…		…
746		815
747	=item $packed_value = $device->info ($name)	816	=item $packed_value = $device->info ($name)
748		817
749	See C<< $platform->info >> for details.	818	See C<< $platform->info >> for details.
750		819
		820	type: OpenCL::DEVICE_TYPE_DEFAULT, OpenCL::DEVICE_TYPE_CPU,
		821	OpenCL::DEVICE_TYPE_GPU, OpenCL::DEVICE_TYPE_ACCELERATOR,
		822	OpenCL::DEVICE_TYPE_CUSTOM, OpenCL::DEVICE_TYPE_ALL.
		823
		824	fp_config: OpenCL::FP_DENORM, OpenCL::FP_INF_NAN, OpenCL::FP_ROUND_TO_NEAREST,
		825	OpenCL::FP_ROUND_TO_ZERO, OpenCL::FP_ROUND_TO_INF, OpenCL::FP_FMA,
		826	OpenCL::FP_SOFT_FLOAT, OpenCL::FP_CORRECTLY_ROUNDED_DIVIDE_SQRT.
		827
		828	mem_cache_type: OpenCL::NONE, OpenCL::READ_ONLY_CACHE, OpenCL::READ_WRITE_CACHE.
		829
		830	local_mem_type: OpenCL::LOCAL, OpenCL::GLOBAL.
		831
		832	exec_capabilities: OpenCL::EXEC_KERNEL, OpenCL::EXEC_NATIVE_KERNEL.
		833
		834	command_queue_properties: OpenCL::QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE,
		835	OpenCL::QUEUE_PROFILING_ENABLE.
		836
		837	partition_properties: OpenCL::DEVICE_PARTITION_EQUALLY,
		838	OpenCL::DEVICE_PARTITION_BY_COUNTS, OpenCL::DEVICE_PARTITION_BY_COUNTS_LIST_END,
		839	OpenCL::DEVICE_PARTITION_BY_AFFINITY_DOMAIN.
		840
		841	affinity_domain: OpenCL::DEVICE_AFFINITY_DOMAIN_NUMA,
		842	OpenCL::DEVICE_AFFINITY_DOMAIN_L4_CACHE, OpenCL::DEVICE_AFFINITY_DOMAIN_L3_CACHE,
		843	OpenCL::DEVICE_AFFINITY_DOMAIN_L2_CACHE, OpenCL::DEVICE_AFFINITY_DOMAIN_L1_CACHE,
		844	OpenCL::DEVICE_AFFINITY_DOMAIN_NEXT_PARTITIONABLE.
		845
751	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetDeviceInfo.html>	846	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetDeviceInfo.html>
752		847
		848	=item @devices = $device->sub_devices (\@properties)
		849
		850	Creates OpencL::SubDevice objects by partitioning an existing device.
		851
		852	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateSubDevices.html>
		853
753	=for gengetinfo begin device	854	=for gengetinfo begin device
754		855
755	=item $device_type = $device->type	856	=item $device_type = $device->type
756		857
757	Calls C<clGetDeviceInfo> with C<CL_DEVICE_TYPE> and returns the result.	858	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_TYPE> and returns the result.
758		859
759	=item $uint = $device->vendor_id	860	=item $uint = $device->vendor_id
760		861
761	Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR_ID> and returns the result.	862	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_VENDOR_ID> and returns the result.
762		863
763	=item $uint = $device->max_compute_units	864	=item $uint = $device->max_compute_units
764		865
765	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_COMPUTE_UNITS> and returns the result.	866	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_COMPUTE_UNITS> and returns the result.
766		867
767	=item $uint = $device->max_work_item_dimensions	868	=item $uint = $device->max_work_item_dimensions
768		869
769	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS> and returns the result.	870	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_WORK_ITEM_DIMENSIONS> and returns the result.
770		871
771	=item $int = $device->max_work_group_size	872	=item $int = $device->max_work_group_size
772		873
773	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_GROUP_SIZE> and returns the result.	874	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_WORK_GROUP_SIZE> and returns the result.
774		875
775	=item @ints = $device->max_work_item_sizes	876	=item @ints = $device->max_work_item_sizes
776		877
777	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_SIZES> and returns the result.	878	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_WORK_ITEM_SIZES> and returns the result.
778		879
779	=item $uint = $device->preferred_vector_width_char	880	=item $uint = $device->preferred_vector_width_char
780		881
781	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR> and returns the result.	882	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_CHAR> and returns the result.
782		883
783	=item $uint = $device->preferred_vector_width_short	884	=item $uint = $device->preferred_vector_width_short
784		885
785	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT> and returns the result.	886	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_SHORT> and returns the result.
786		887
787	=item $uint = $device->preferred_vector_width_int	888	=item $uint = $device->preferred_vector_width_int
788		889
789	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT> and returns the result.	890	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_INT> and returns the result.
790		891
791	=item $uint = $device->preferred_vector_width_long	892	=item $uint = $device->preferred_vector_width_long
792		893
793	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG> and returns the result.	894	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_LONG> and returns the result.
794		895
795	=item $uint = $device->preferred_vector_width_float	896	=item $uint = $device->preferred_vector_width_float
796		897
797	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT> and returns the result.	898	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT> and returns the result.
798		899
799	=item $uint = $device->preferred_vector_width_double	900	=item $uint = $device->preferred_vector_width_double
800		901
801	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE> and returns the result.	902	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE> and returns the result.
802		903
803	=item $uint = $device->max_clock_frequency	904	=item $uint = $device->max_clock_frequency
804		905
805	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CLOCK_FREQUENCY> and returns the result.	906	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_CLOCK_FREQUENCY> and returns the result.
806		907
807	=item $bitfield = $device->address_bits	908	=item $bitfield = $device->address_bits
808		909
809	Calls C<clGetDeviceInfo> with C<CL_DEVICE_ADDRESS_BITS> and returns the result.	910	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_ADDRESS_BITS> and returns the result.
810		911
811	=item $uint = $device->max_read_image_args	912	=item $uint = $device->max_read_image_args
812		913
813	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_READ_IMAGE_ARGS> and returns the result.	914	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_READ_IMAGE_ARGS> and returns the result.
814		915
815	=item $uint = $device->max_write_image_args	916	=item $uint = $device->max_write_image_args
816		917
817	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WRITE_IMAGE_ARGS> and returns the result.	918	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_WRITE_IMAGE_ARGS> and returns the result.
818		919
819	=item $ulong = $device->max_mem_alloc_size	920	=item $ulong = $device->max_mem_alloc_size
820		921
821	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_MEM_ALLOC_SIZE> and returns the result.	922	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_MEM_ALLOC_SIZE> and returns the result.
822		923
823	=item $int = $device->image2d_max_width	924	=item $int = $device->image2d_max_width
824		925
825	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_WIDTH> and returns the result.	926	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE2D_MAX_WIDTH> and returns the result.
826		927
827	=item $int = $device->image2d_max_height	928	=item $int = $device->image2d_max_height
828		929
829	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_HEIGHT> and returns the result.	930	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE2D_MAX_HEIGHT> and returns the result.
830		931
831	=item $int = $device->image3d_max_width	932	=item $int = $device->image3d_max_width
832		933
833	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_WIDTH> and returns the result.	934	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE3D_MAX_WIDTH> and returns the result.
834		935
835	=item $int = $device->image3d_max_height	936	=item $int = $device->image3d_max_height
836		937
837	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_HEIGHT> and returns the result.	938	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE3D_MAX_HEIGHT> and returns the result.
838		939
839	=item $int = $device->image3d_max_depth	940	=item $int = $device->image3d_max_depth
840		941
841	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_DEPTH> and returns the result.	942	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE3D_MAX_DEPTH> and returns the result.
842		943
843	=item $uint = $device->image_support	944	=item $uint = $device->image_support
844		945
845	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE_SUPPORT> and returns the result.	946	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE_SUPPORT> and returns the result.
846		947
847	=item $int = $device->max_parameter_size	948	=item $int = $device->max_parameter_size
848		949
849	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_PARAMETER_SIZE> and returns the result.	950	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_PARAMETER_SIZE> and returns the result.
850		951
851	=item $uint = $device->max_samplers	952	=item $uint = $device->max_samplers
852		953
853	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_SAMPLERS> and returns the result.	954	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_SAMPLERS> and returns the result.
854		955
855	=item $uint = $device->mem_base_addr_align	956	=item $uint = $device->mem_base_addr_align
856		957
857	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MEM_BASE_ADDR_ALIGN> and returns the result.	958	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MEM_BASE_ADDR_ALIGN> and returns the result.
858		959
859	=item $uint = $device->min_data_type_align_size	960	=item $uint = $device->min_data_type_align_size
860		961
861	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE> and returns the result.	962	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MIN_DATA_TYPE_ALIGN_SIZE> and returns the result.
862		963
863	=item $device_fp_config = $device->single_fp_config	964	=item $device_fp_config = $device->single_fp_config
864		965
865	Calls C<clGetDeviceInfo> with C<CL_DEVICE_SINGLE_FP_CONFIG> and returns the result.	966	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_SINGLE_FP_CONFIG> and returns the result.
866		967
867	=item $device_mem_cache_type = $device->global_mem_cache_type	968	=item $device_mem_cache_type = $device->global_mem_cache_type
868		969
869	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_TYPE> and returns the result.	970	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_GLOBAL_MEM_CACHE_TYPE> and returns the result.
870		971
871	=item $uint = $device->global_mem_cacheline_size	972	=item $uint = $device->global_mem_cacheline_size
872		973
873	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE> and returns the result.	974	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_GLOBAL_MEM_CACHELINE_SIZE> and returns the result.
874		975
875	=item $ulong = $device->global_mem_cache_size	976	=item $ulong = $device->global_mem_cache_size
876		977
877	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_SIZE> and returns the result.	978	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_GLOBAL_MEM_CACHE_SIZE> and returns the result.
878		979
879	=item $ulong = $device->global_mem_size	980	=item $ulong = $device->global_mem_size
880		981
881	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_SIZE> and returns the result.	982	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_GLOBAL_MEM_SIZE> and returns the result.
882		983
883	=item $ulong = $device->max_constant_buffer_size	984	=item $ulong = $device->max_constant_buffer_size
884		985
885	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE> and returns the result.	986	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_CONSTANT_BUFFER_SIZE> and returns the result.
886		987
887	=item $uint = $device->max_constant_args	988	=item $uint = $device->max_constant_args
888		989
889	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_ARGS> and returns the result.	990	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_CONSTANT_ARGS> and returns the result.
890		991
891	=item $device_local_mem_type = $device->local_mem_type	992	=item $device_local_mem_type = $device->local_mem_type
892		993
893	Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_TYPE> and returns the result.	994	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_LOCAL_MEM_TYPE> and returns the result.
894		995
895	=item $ulong = $device->local_mem_size	996	=item $ulong = $device->local_mem_size
896		997
897	Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_SIZE> and returns the result.	998	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_LOCAL_MEM_SIZE> and returns the result.
898		999
899	=item $boolean = $device->error_correction_support	1000	=item $boolean = $device->error_correction_support
900		1001
901	Calls C<clGetDeviceInfo> with C<CL_DEVICE_ERROR_CORRECTION_SUPPORT> and returns the result.	1002	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_ERROR_CORRECTION_SUPPORT> and returns the result.
902		1003
903	=item $int = $device->profiling_timer_resolution	1004	=item $int = $device->profiling_timer_resolution
904		1005
905	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILING_TIMER_RESOLUTION> and returns the result.	1006	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PROFILING_TIMER_RESOLUTION> and returns the result.
906		1007
907	=item $boolean = $device->endian_little	1008	=item $boolean = $device->endian_little
908		1009
909	Calls C<clGetDeviceInfo> with C<CL_DEVICE_ENDIAN_LITTLE> and returns the result.	1010	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_ENDIAN_LITTLE> and returns the result.
910		1011
911	=item $boolean = $device->available	1012	=item $boolean = $device->available
912		1013
913	Calls C<clGetDeviceInfo> with C<CL_DEVICE_AVAILABLE> and returns the result.	1014	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_AVAILABLE> and returns the result.
914		1015
915	=item $boolean = $device->compiler_available	1016	=item $boolean = $device->compiler_available
916		1017
917	Calls C<clGetDeviceInfo> with C<CL_DEVICE_COMPILER_AVAILABLE> and returns the result.	1018	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_COMPILER_AVAILABLE> and returns the result.
918		1019
919	=item $device_exec_capabilities = $device->execution_capabilities	1020	=item $device_exec_capabilities = $device->execution_capabilities
920		1021
921	Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXECUTION_CAPABILITIES> and returns the result.	1022	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_EXECUTION_CAPABILITIES> and returns the result.
922		1023
923	=item $command_queue_properties = $device->properties	1024	=item $command_queue_properties = $device->properties
924		1025
925	Calls C<clGetDeviceInfo> with C<CL_DEVICE_QUEUE_PROPERTIES> and returns the result.	1026	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_QUEUE_PROPERTIES> and returns the result.
926		1027
927	=item $ = $device->platform	1028	=item $ = $device->platform
928		1029
929	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PLATFORM> and returns the result.	1030	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PLATFORM> and returns the result.
930		1031
931	=item $string = $device->name	1032	=item $string = $device->name
932		1033
933	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NAME> and returns the result.	1034	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NAME> and returns the result.
934		1035
935	=item $string = $device->vendor	1036	=item $string = $device->vendor
936		1037
937	Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR> and returns the result.	1038	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_VENDOR> and returns the result.
938		1039
939	=item $string = $device->driver_version	1040	=item $string = $device->driver_version
940		1041
941	Calls C<clGetDeviceInfo> with C<CL_DRIVER_VERSION> and returns the result.	1042	Calls C<clGetDeviceInfo> with C<OpenCL::DRIVER_VERSION> and returns the result.
942		1043
943	=item $string = $device->profile	1044	=item $string = $device->profile
944		1045
945	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILE> and returns the result.	1046	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PROFILE> and returns the result.
946		1047
947	=item $string = $device->version	1048	=item $string = $device->version
948		1049
949	Calls C<clGetDeviceInfo> with C<CL_DEVICE_VERSION> and returns the result.	1050	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_VERSION> and returns the result.
950		1051
951	=item $string = $device->extensions	1052	=item $string = $device->extensions
952		1053
953	Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXTENSIONS> and returns the result.	1054	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_EXTENSIONS> and returns the result.
954		1055
955	=item $uint = $device->preferred_vector_width_half	1056	=item $uint = $device->preferred_vector_width_half
956		1057
957	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF> and returns the result.	1058	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_HALF> and returns the result.
958		1059
959	=item $uint = $device->native_vector_width_char	1060	=item $uint = $device->native_vector_width_char
960		1061
961	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR> and returns the result.	1062	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_CHAR> and returns the result.
962		1063
963	=item $uint = $device->native_vector_width_short	1064	=item $uint = $device->native_vector_width_short
964		1065
965	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT> and returns the result.	1066	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_SHORT> and returns the result.
966		1067
967	=item $uint = $device->native_vector_width_int	1068	=item $uint = $device->native_vector_width_int
968		1069
969	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_INT> and returns the result.	1070	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_INT> and returns the result.
970		1071
971	=item $uint = $device->native_vector_width_long	1072	=item $uint = $device->native_vector_width_long
972		1073
973	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG> and returns the result.	1074	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_LONG> and returns the result.
974		1075
975	=item $uint = $device->native_vector_width_float	1076	=item $uint = $device->native_vector_width_float
976		1077
977	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT> and returns the result.	1078	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_FLOAT> and returns the result.
978		1079
979	=item $uint = $device->native_vector_width_double	1080	=item $uint = $device->native_vector_width_double
980		1081
981	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE> and returns the result.	1082	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE> and returns the result.
982		1083
983	=item $uint = $device->native_vector_width_half	1084	=item $uint = $device->native_vector_width_half
984		1085
985	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF> and returns the result.	1086	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_HALF> and returns the result.
986		1087
987	=item $device_fp_config = $device->double_fp_config	1088	=item $device_fp_config = $device->double_fp_config
988		1089
989	Calls C<clGetDeviceInfo> with C<CL_DEVICE_DOUBLE_FP_CONFIG> and returns the result.	1090	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_DOUBLE_FP_CONFIG> and returns the result.
990		1091
991	=item $device_fp_config = $device->half_fp_config	1092	=item $device_fp_config = $device->half_fp_config
992		1093
993	Calls C<clGetDeviceInfo> with C<CL_DEVICE_HALF_FP_CONFIG> and returns the result.	1094	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_HALF_FP_CONFIG> and returns the result.
994		1095
995	=item $boolean = $device->host_unified_memory	1096	=item $boolean = $device->host_unified_memory
996		1097
997	Calls C<clGetDeviceInfo> with C<CL_DEVICE_HOST_UNIFIED_MEMORY> and returns the result.	1098	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_HOST_UNIFIED_MEMORY> and returns the result.
998		1099
999	=item $device = $device->parent_device_ext	1100	=item $device = $device->parent_device_ext
1000		1101
1001	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARENT_DEVICE_EXT> and returns the result.	1102	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PARENT_DEVICE_EXT> and returns the result.
1002		1103
1003	=item @device_partition_property_exts = $device->partition_types_ext	1104	=item @device_partition_property_exts = $device->partition_types_ext
1004		1105
1005	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_TYPES_EXT> and returns the result.	1106	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PARTITION_TYPES_EXT> and returns the result.
1006		1107
1007	=item @device_partition_property_exts = $device->affinity_domains_ext	1108	=item @device_partition_property_exts = $device->affinity_domains_ext
1008		1109
1009	Calls C<clGetDeviceInfo> with C<CL_DEVICE_AFFINITY_DOMAINS_EXT> and returns the result.	1110	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_AFFINITY_DOMAINS_EXT> and returns the result.
1010		1111
1011	=item $uint = $device->reference_count_ext	1112	=item $uint = $device->reference_count_ext
1012		1113
1013	Calls C<clGetDeviceInfo> with C<CL_DEVICE_REFERENCE_COUNT_EXT> and returns the result.	1114	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_REFERENCE_COUNT_EXT> and returns the result.
1014		1115
1015	=item @device_partition_property_exts = $device->partition_style_ext	1116	=item @device_partition_property_exts = $device->partition_style_ext
1016		1117
1017	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_STYLE_EXT> and returns the result.	1118	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PARTITION_STYLE_EXT> and returns the result.
1018		1119
1019	=for gengetinfo end device	1120	=for gengetinfo end device
1020		1121
1021	=back	1122	=back
1022		1123
1023	=head2 THE OpenCL::Context CLASS	1124	=head2 THE OpenCL::Context CLASS
		1125
		1126	An OpenCL::Context is basically a container, or manager, for a number of
		1127	devices of a platform. It is used to create all sorts of secondary objects
		1128	such as buffers, queues, programs and so on.
		1129
		1130	All context creation functions and methods take a list of properties
		1131	(type-value pairs). All property values can be specified as integers -
		1132	some additionally support other types:
		1133
		1134	=over 4
		1135
		1136	=item OpenCL::CONTEXT_PLATFORM
		1137
		1138	Also accepts OpenCL::Platform objects.
		1139
		1140	=item OpenCL::GLX_DISPLAY_KHR
		1141
		1142	Also accepts C<undef>, in which case a deep and troubling hack is engaged
		1143	to find the current glx display (see L<GLX SUPPORT>).
		1144
		1145	=item OpenCL::GL_CONTEXT_KHR
		1146
		1147	Also accepts C<undef>, in which case a deep and troubling hack is engaged
		1148	to find the current glx context (see L<GLX SUPPORT>).
		1149
		1150	=back
1024		1151
1025	=over 4	1152	=over 4
1026		1153
1027	=item $prog = $ctx->build_program ($program, $options = "")	1154	=item $prog = $ctx->build_program ($program, $options = "")
1028		1155
…		…
1076	=item $buf = $ctx->buffer ($flags, $len)	1203	=item $buf = $ctx->buffer ($flags, $len)
1077		1204
1078	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object with the	1205	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object with the
1079	given flags and octet-size.	1206	given flags and octet-size.
1080		1207
		1208	flags: OpenCL::MEM_READ_WRITE, OpenCL::MEM_WRITE_ONLY, OpenCL::MEM_READ_ONLY,
		1209	OpenCL::MEM_USE_HOST_PTR, OpenCL::MEM_ALLOC_HOST_PTR, OpenCL::MEM_COPY_HOST_PTR,
		1210	OpenCL::MEM_HOST_WRITE_ONLY, OpenCL::MEM_HOST_READ_ONLY, OpenCL::MEM_HOST_NO_ACCESS.
		1211
1081	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateBuffer.html>	1212	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateBuffer.html>
1082		1213
1083	=item $buf = $ctx->buffer_sv ($flags, $data)	1214	=item $buf = $ctx->buffer_sv ($flags, $data)
1084		1215
1085	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object and	1216	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object and
…		…
1088	=item $img = $ctx->image ($self, $flags, $channel_order, $channel_type, $type, $width, $height, $depth = 0, $array_size = 0, $row_pitch = 0, $slice_pitch = 0, $num_mip_level = 0, $num_samples = 0, $*data = &PL_sv_undef)	1219	=item $img = $ctx->image ($self, $flags, $channel_order, $channel_type, $type, $width, $height, $depth = 0, $array_size = 0, $row_pitch = 0, $slice_pitch = 0, $num_mip_level = 0, $num_samples = 0, $*data = &PL_sv_undef)
1089		1220
1090	Creates a new OpenCL::Image object and optionally initialises it with	1221	Creates a new OpenCL::Image object and optionally initialises it with
1091	the given data values.	1222	the given data values.
1092		1223
		1224	channel_order: OpenCL::R, OpenCL::A, OpenCL::RG, OpenCL::RA, OpenCL::RGB,
		1225	OpenCL::RGBA, OpenCL::BGRA, OpenCL::ARGB, OpenCL::INTENSITY, OpenCL::LUMINANCE,
		1226	OpenCL::Rx, OpenCL::RGx, OpenCL::RGBx.
		1227
		1228	channel_type: OpenCL::SNORM_INT8, OpenCL::SNORM_INT16, OpenCL::UNORM_INT8,
		1229	OpenCL::UNORM_INT16, OpenCL::UNORM_SHORT_565, OpenCL::UNORM_SHORT_555,
		1230	OpenCL::UNORM_INT_101010, OpenCL::SIGNED_INT8, OpenCL::SIGNED_INT16,
		1231	OpenCL::SIGNED_INT32, OpenCL::UNSIGNED_INT8, OpenCL::UNSIGNED_INT16,
		1232	OpenCL::UNSIGNED_INT32, OpenCL::HALF_FLOAT, OpenCL::FLOAT.
		1233
		1234	type: OpenCL::MEM_OBJECT_BUFFER, OpenCL::MEM_OBJECT_IMAGE2D,
		1235	OpenCL::MEM_OBJECT_IMAGE3D, OpenCL::MEM_OBJECT_IMAGE2D_ARRAY,
		1236	OpenCL::MEM_OBJECT_IMAGE1D, OpenCL::MEM_OBJECT_IMAGE1D_ARRAY,
		1237	OpenCL::MEM_OBJECT_IMAGE1D_BUFFER.
		1238
1093	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateImage.html>	1239	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateImage.html>
1094		1240
1095	=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef)	1241	=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef)
1096		1242
1097	Creates a new OpenCL::Image2D object and optionally initialises it with	1243	Creates a new OpenCL::Image2D object and optionally initialises it with
…		…
1109	=item $buffer = $ctx->gl_buffer ($flags, $bufobj)	1255	=item $buffer = $ctx->gl_buffer ($flags, $bufobj)
1110		1256
1111	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object that refers to the given	1257	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object that refers to the given
1112	OpenGL buffer object.	1258	OpenGL buffer object.
1113		1259
		1260	flags: OpenCL::MEM_READ_WRITE, OpenCL::MEM_READ_ONLY, OpenCL::MEM_WRITE_ONLY.
		1261
1114	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLBuffer.html	1262	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLBuffer.html
1115		1263
1116	=item $img = $ctx->gl_texture ($flags, $target, $miplevel, $texture)	1264	=item $img = $ctx->gl_texture ($flags, $target, $miplevel, $texture)
1117		1265
1118	Creates a new OpenCL::Image object that refers to the given OpenGL	1266	Creates a new OpenCL::Image object that refers to the given OpenGL
1119	texture object or buffer.	1267	texture object or buffer.
1120		1268
		1269	target: GL_TEXTURE_1D, GL_TEXTURE_1D_ARRAY, GL_TEXTURE_BUFFER,
		1270	GL_TEXTURE_2D, GL_TEXTURE_2D_ARRAY, GL_TEXTURE_3D,
		1271	GL_TEXTURE_CUBE_MAP_POSITIVE_X, GL_TEXTURE_CUBE_MAP_POSITIVE_Y,
		1272	GL_TEXTURE_CUBE_MAP_POSITIVE_Z, GL_TEXTURE_CUBE_MAP_NEGATIVE_X,
		1273	GL_TEXTURE_CUBE_MAP_NEGATIVE_Y, GL_TEXTURE_CUBE_MAP_NEGATIVE_Z,
		1274	GL_TEXTURE_RECTANGLE/GL_TEXTURE_RECTANGLE_ARB.
		1275
1121	http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateFromGLTexture.html	1276	http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateFromGLTexture.html
1122		1277
1123	=item $img = $ctx->gl_texture2d ($flags, $target, $miplevel, $texture)	1278	=item $img = $ctx->gl_texture2d ($flags, $target, $miplevel, $texture)
1124		1279
1125	Creates a new OpenCL::Image2D object that refers to the given OpenGL	1280	Creates a new OpenCL::Image2D object that refers to the given OpenGL
…		…
1150		1305
1151	=item $sampler = $ctx->sampler ($normalized_coords, $addressing_mode, $filter_mode)	1306	=item $sampler = $ctx->sampler ($normalized_coords, $addressing_mode, $filter_mode)
1152		1307
1153	Creates a new OpenCL::Sampler object.	1308	Creates a new OpenCL::Sampler object.
1154		1309
		1310	addressing_mode: OpenCL::ADDRESS_NONE, OpenCL::ADDRESS_CLAMP_TO_EDGE,
		1311	OpenCL::ADDRESS_CLAMP, OpenCL::ADDRESS_REPEAT, OpenCL::ADDRESS_MIRRORED_REPEAT.
		1312
		1313	filter_mode: OpenCL::FILTER_NEAREST, OpenCL::FILTER_LINEAR.
		1314
1155	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSampler.html>	1315	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSampler.html>
1156		1316
1157	=item $program = $ctx->program_with_source ($string)	1317	=item $program = $ctx->program_with_source ($string)
1158		1318
1159	Creates a new OpenCL::Program object from the given source code.	1319	Creates a new OpenCL::Program object from the given source code.
1160		1320
1161	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateProgramWithSource.html>	1321	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateProgramWithSource.html>
1162		1322
		1323	=item ($program, \@status) = $ctx->program_with_binary (\@devices, \@binaries)
		1324
		1325	Creates a new OpenCL::Program object from the given binaries.
		1326
		1327	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateProgramWithBinary.html>
		1328
		1329	Example: clone an existing program object that contains a successfully
		1330	compiled program, no matter how useless this is.
		1331
		1332	my $clone = $ctx->program_with_binary ([$prog->devices], [$prog->binaries]);
		1333
		1334	=item $program = $ctx->program_with_built_in_kernels (\@devices, $kernel_names)
		1335
		1336	Creates a new OpenCL::Program object from the given built-in kernel names.
		1337
		1338	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateProgramWithBuiltInKernels.html>
		1339
		1340	=item $program = $ctx->link_program (\@devices, $options, \@programs, $cb->($program) = undef)
		1341
		1342	Links all (already compiled) program objects specified in C<@programs>
		1343	together and returns a new OpenCL::Program object with the result.
		1344
		1345	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clLinkProgram.html>
		1346
1163	=item $packed_value = $ctx->info ($name)	1347	=item $packed_value = $ctx->info ($name)
1164		1348
1165	See C<< $platform->info >> for details.	1349	See C<< $platform->info >> for details.
1166		1350
1167	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetContextInfo.html>	1351	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetContextInfo.html>
1168		1352
1169	=for gengetinfo begin context	1353	=for gengetinfo begin context
1170		1354
1171	=item $uint = $context->reference_count	1355	=item $uint = $context->reference_count
1172		1356
1173	Calls C<clGetContextInfo> with C<CL_CONTEXT_REFERENCE_COUNT> and returns the result.	1357	Calls C<clGetContextInfo> with C<OpenCL::CONTEXT_REFERENCE_COUNT> and returns the result.
1174		1358
1175	=item @devices = $context->devices	1359	=item @devices = $context->devices
1176		1360
1177	Calls C<clGetContextInfo> with C<CL_CONTEXT_DEVICES> and returns the result.	1361	Calls C<clGetContextInfo> with C<OpenCL::CONTEXT_DEVICES> and returns the result.
1178		1362
1179	=item @property_ints = $context->properties	1363	=item @property_ints = $context->properties
1180		1364
1181	Calls C<clGetContextInfo> with C<CL_CONTEXT_PROPERTIES> and returns the result.	1365	Calls C<clGetContextInfo> with C<OpenCL::CONTEXT_PROPERTIES> and returns the result.
1182		1366
1183	=item $uint = $context->num_devices	1367	=item $uint = $context->num_devices
1184		1368
1185	Calls C<clGetContextInfo> with C<CL_CONTEXT_NUM_DEVICES> and returns the result.	1369	Calls C<clGetContextInfo> with C<OpenCL::CONTEXT_NUM_DEVICES> and returns the result.
1186		1370
1187	=for gengetinfo end context	1371	=for gengetinfo end context
1188		1372
1189	=back	1373	=back
1190		1374
…		…
1306	reference to an array of local work sizes, with the same number of	1490	reference to an array of local work sizes, with the same number of
1307	elements as \@global_work_size.	1491	elements as \@global_work_size.
1308		1492
1309	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html>	1493	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html>
1310		1494
		1495	=item $ev = $queue->migrate_mem_objects (\@mem_objects, $flags, $wait_events...)
		1496
		1497	Migrates a number of OpenCL::Memory objects to or from the device.
		1498
		1499	flags: OpenCL::MIGRATE_MEM_OBJECT_HOST, OpenCL::MIGRATE_MEM_OBJECT_CONTENT_UNDEFINED
		1500
		1501	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueMigrateMemObjects.html>
		1502
1311	=item $ev = $queue->acquire_gl_objects ([object, ...], $wait_events...)	1503	=item $ev = $queue->acquire_gl_objects ([object, ...], $wait_events...)
1312		1504
1313	Enqueues a list (an array-ref of OpenCL::Memory objects) to be acquired	1505	Enqueues a list (an array-ref of OpenCL::Memory objects) to be acquired
1314	for subsequent OpenCL usage.	1506	for subsequent OpenCL usage.
1315		1507
…		…
1350		1542
1351	=for gengetinfo begin command_queue	1543	=for gengetinfo begin command_queue
1352		1544
1353	=item $ctx = $command_queue->context	1545	=item $ctx = $command_queue->context
1354		1546
1355	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_CONTEXT> and returns the result.	1547	Calls C<clGetCommandQueueInfo> with C<OpenCL::QUEUE_CONTEXT> and returns the result.
1356		1548
1357	=item $device = $command_queue->device	1549	=item $device = $command_queue->device
1358		1550
1359	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_DEVICE> and returns the result.	1551	Calls C<clGetCommandQueueInfo> with C<OpenCL::QUEUE_DEVICE> and returns the result.
1360		1552
1361	=item $uint = $command_queue->reference_count	1553	=item $uint = $command_queue->reference_count
1362		1554
1363	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_REFERENCE_COUNT> and returns the result.	1555	Calls C<clGetCommandQueueInfo> with C<OpenCL::QUEUE_REFERENCE_COUNT> and returns the result.
1364		1556
1365	=item $command_queue_properties = $command_queue->properties	1557	=item $command_queue_properties = $command_queue->properties
1366		1558
1367	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_PROPERTIES> and returns the result.	1559	Calls C<clGetCommandQueueInfo> with C<OpenCL::QUEUE_PROPERTIES> and returns the result.
1368		1560
1369	=for gengetinfo end command_queue	1561	=for gengetinfo end command_queue
1370		1562
1371	=back	1563	=back
1372		1564
…		…
1374		1566
1375	OpenCL allows you to map buffers and images to host memory (read: perl	1567	OpenCL allows you to map buffers and images to host memory (read: perl
1376	scalars). This is done much like reading or copying a buffer, by enqueuing	1568	scalars). This is done much like reading or copying a buffer, by enqueuing
1377	a map or unmap operation on the command queue.	1569	a map or unmap operation on the command queue.
1378		1570
1379	The map operations return a C<OpenCL::Mapped> object - see L<THE	1571	The map operations return an C<OpenCL::Mapped> object - see L<THE
1380	OpenCL::Mapped CLASS> section for details on what to do with these	1572	OpenCL::Mapped CLASS> section for details on what to do with these
1381	objects.	1573	objects.
1382		1574
1383	The object will be unmapped automatically when the mapped object is	1575	The object will be unmapped automatically when the mapped object is
1384	destroyed (you can use a barrier to make sure the unmap has finished,	1576	destroyed (you can use a barrier to make sure the unmap has finished,
1385	before using the buffer in a kernel), but you can also enqueue an unmap	1577	before using the buffer in a kernel), but you can also enqueue an unmap
1386	operation manually.	1578	operation manually.
1387		1579
1388	=over 4	1580	=over 4
1389		1581
1390	=item $mapped_buffer = $queue->map_buffer ($buf, $data, $blocking=1, $map_flags=OpenCL::MAP_READ\|OpenCL::MAP_WRITE, $offset=0, $size=0, $wait_events...)	1582	=item $mapped_buffer = $queue->map_buffer ($buf, $blocking=1, $map_flags=OpenCL::MAP_READ\|OpenCL::MAP_WRITE, $offset=0, $size=undef, $wait_events...)
1391		1583
1392	Maps the given buffer into host memory and returns a C<OpenCL::MappedBuffer> object.	1584	Maps the given buffer into host memory and returns an
		1585	C<OpenCL::MappedBuffer> object. If C<$size> is specified as undef, then
		1586	the map will extend to the end of the buffer.
		1587
		1588	map_flags: OpenCL::MAP_READ, OpenCL::MAP_WRITE, OpenCL::MAP_WRITE_INVALIDATE_REGION.
1393		1589
1394	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMapBuffer.html>	1590	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMapBuffer.html>
1395		1591
		1592	Example: map the buffer $buf fully and replace the first 4 bytes by "abcd", then unmap.
		1593
		1594	{
		1595	my $mapped = $queue->map_buffer ($buf, 1, OpenCL::MAP_WRITE);
		1596	substr $$mapped, 0, 4, "abcd";
		1597	} # asynchronously unmap because $mapped is destroyed
		1598
1396	=item $mapped_image = $queue->map_image ($img, $data, $blocking=1, $map_flags=OpenCL::MAP_READ\|OpenCL::MAP_WRITE, $x=0, $y=0, $z=0, $width=0, $height=0, $depth=0, $wait_events...)	1599	=item $mapped_image = $queue->map_image ($img, $blocking=1, $map_flags=OpenCL::MAP_READ\|OpenCL::MAP_WRITE, $x=0, $y=0, $z=0, $width=undef, $height=undef, $depth=undef, $wait_events...)
1397		1600
1398	Maps the given image area into host memory and return a	1601	Maps the given image area into host memory and return an
1399	C<OpenCL::MappedImage> object. Although there are default values for most	1602	C<OpenCL::MappedImage> object.
1400	arguments, you currently have to specify all arguments, otherwise the call	1603
1401	will fail.	1604	If any of C<$width>, C<$height> and/or C<$depth> are C<undef> then they
		1605	will be replaced by the maximum possible value.
1402		1606
1403	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMapImage.html>	1607	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMapImage.html>
		1608
		1609	Example: map an image (with OpenCL::UNSIGNED_INT8 channel type) and set
		1610	the first channel of the leftmost column to 5, then explicitly unmap
		1611	it. You are not necessarily meant to do it this way, this example just
		1612	shows you the accessors to use :)
		1613
		1614	my $mapped = $queue->map_image ($image, 1, OpenCL::MAP_WRITE);
		1615
		1616	$mapped->set ($_ * $mapped->row_pitch, pack "C", 5)
		1617	for 0..$image->height;
		1618
		1619	$mapped->unmap;.
		1620	$mapped->wait; # only needed for out of order queues normally
1404		1621
1405	=item $ev = $queue->unmap ($mapped, $wait_events...)	1622	=item $ev = $queue->unmap ($mapped, $wait_events...)
1406		1623
1407	Unmaps the data from host memory. You must not call any methods that	1624	Unmaps the data from host memory. You must not call any methods that
1408	modify the data, or modify the data scalar directly, after calling this	1625	modify the data, or modify the data scalar directly, after calling this
…		…
1429		1646
1430	=for gengetinfo begin mem	1647	=for gengetinfo begin mem
1431		1648
1432	=item $mem_object_type = $mem->type	1649	=item $mem_object_type = $mem->type
1433		1650
1434	Calls C<clGetMemObjectInfo> with C<CL_MEM_TYPE> and returns the result.	1651	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_TYPE> and returns the result.
1435		1652
1436	=item $mem_flags = $mem->flags	1653	=item $mem_flags = $mem->flags
1437		1654
1438	Calls C<clGetMemObjectInfo> with C<CL_MEM_FLAGS> and returns the result.	1655	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_FLAGS> and returns the result.
1439		1656
1440	=item $int = $mem->size	1657	=item $int = $mem->size
1441		1658
1442	Calls C<clGetMemObjectInfo> with C<CL_MEM_SIZE> and returns the result.	1659	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_SIZE> and returns the result.
1443		1660
1444	=item $ptr_value = $mem->host_ptr	1661	=item $ptr_value = $mem->host_ptr
1445		1662
1446	Calls C<clGetMemObjectInfo> with C<CL_MEM_HOST_PTR> and returns the result.	1663	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_HOST_PTR> and returns the result.
1447		1664
1448	=item $uint = $mem->map_count	1665	=item $uint = $mem->map_count
1449		1666
1450	Calls C<clGetMemObjectInfo> with C<CL_MEM_MAP_COUNT> and returns the result.	1667	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_MAP_COUNT> and returns the result.
1451		1668
1452	=item $uint = $mem->reference_count	1669	=item $uint = $mem->reference_count
1453		1670
1454	Calls C<clGetMemObjectInfo> with C<CL_MEM_REFERENCE_COUNT> and returns the result.	1671	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_REFERENCE_COUNT> and returns the result.
1455		1672
1456	=item $ctx = $mem->context	1673	=item $ctx = $mem->context
1457		1674
1458	Calls C<clGetMemObjectInfo> with C<CL_MEM_CONTEXT> and returns the result.	1675	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_CONTEXT> and returns the result.
1459		1676
1460	=item $mem = $mem->associated_memobject	1677	=item $mem = $mem->associated_memobject
1461		1678
1462	Calls C<clGetMemObjectInfo> with C<CL_MEM_ASSOCIATED_MEMOBJECT> and returns the result.	1679	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_ASSOCIATED_MEMOBJECT> and returns the result.
1463		1680
1464	=item $int = $mem->offset	1681	=item $int = $mem->offset
1465		1682
1466	Calls C<clGetMemObjectInfo> with C<CL_MEM_OFFSET> and returns the result.	1683	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_OFFSET> and returns the result.
1467		1684
1468	=for gengetinfo end mem	1685	=for gengetinfo end mem
1469		1686
1470	=item ($type, $name) = $mem->gl_object_info	1687	=item ($type, $name) = $mem->gl_object_info
1471		1688
…		…
1491	=over 4	1708	=over 4
1492		1709
1493	=item $subbuf = $buf_obj->sub_buffer_region ($flags, $origin, $size)	1710	=item $subbuf = $buf_obj->sub_buffer_region ($flags, $origin, $size)
1494		1711
1495	Creates an OpenCL::Buffer objects from this buffer and returns it. The	1712	Creates an OpenCL::Buffer objects from this buffer and returns it. The
1496	C<buffer_create_type> is assumed to be C<CL_BUFFER_CREATE_TYPE_REGION>.	1713	C<buffer_create_type> is assumed to be C<OpenCL::BUFFER_CREATE_TYPE_REGION>.
1497		1714
1498	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSubBuffer.html>	1715	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSubBuffer.html>
1499		1716
1500	=back	1717	=back
1501		1718
…		…
1517	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetImageInfo.html>	1734	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetImageInfo.html>
1518		1735
1519	=item ($channel_order, $channel_data_type) = $image->format	1736	=item ($channel_order, $channel_data_type) = $image->format
1520		1737
1521	Returns the channel order and type used to create the image by calling	1738	Returns the channel order and type used to create the image by calling
1522	C<clGetImageInfo> with C<CL_IMAGE_FORMAT>.	1739	C<clGetImageInfo> with C<OpenCL::IMAGE_FORMAT>.
1523		1740
1524	=for gengetinfo begin image	1741	=for gengetinfo begin image
1525		1742
1526	=item $int = $image->element_size	1743	=item $int = $image->element_size
1527		1744
1528	Calls C<clGetImageInfo> with C<CL_IMAGE_ELEMENT_SIZE> and returns the result.	1745	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_ELEMENT_SIZE> and returns the result.
1529		1746
1530	=item $int = $image->row_pitch	1747	=item $int = $image->row_pitch
1531		1748
1532	Calls C<clGetImageInfo> with C<CL_IMAGE_ROW_PITCH> and returns the result.	1749	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_ROW_PITCH> and returns the result.
1533		1750
1534	=item $int = $image->slice_pitch	1751	=item $int = $image->slice_pitch
1535		1752
1536	Calls C<clGetImageInfo> with C<CL_IMAGE_SLICE_PITCH> and returns the result.	1753	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_SLICE_PITCH> and returns the result.
1537		1754
1538	=item $int = $image->width	1755	=item $int = $image->width
1539		1756
1540	Calls C<clGetImageInfo> with C<CL_IMAGE_WIDTH> and returns the result.	1757	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_WIDTH> and returns the result.
1541		1758
1542	=item $int = $image->height	1759	=item $int = $image->height
1543		1760
1544	Calls C<clGetImageInfo> with C<CL_IMAGE_HEIGHT> and returns the result.	1761	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_HEIGHT> and returns the result.
1545		1762
1546	=item $int = $image->depth	1763	=item $int = $image->depth
1547		1764
1548	Calls C<clGetImageInfo> with C<CL_IMAGE_DEPTH> and returns the result.	1765	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_DEPTH> and returns the result.
1549		1766
1550	=for gengetinfo end image	1767	=for gengetinfo end image
1551		1768
1552	=for gengetinfo begin gl_texture	1769	=for gengetinfo begin gl_texture
1553		1770
1554	=item $GLenum = $gl_texture->target	1771	=item $GLenum = $gl_texture->target
1555		1772
1556	Calls C<clGetGLTextureInfo> with C<CL_GL_TEXTURE_TARGET> and returns the result.	1773	Calls C<clGetGLTextureInfo> with C<OpenCL::GL_TEXTURE_TARGET> and returns the result.
1557		1774
1558	=item $GLint = $gl_texture->gl_mipmap_level	1775	=item $GLint = $gl_texture->gl_mipmap_level
1559		1776
1560	Calls C<clGetGLTextureInfo> with C<CL_GL_MIPMAP_LEVEL> and returns the result.	1777	Calls C<clGetGLTextureInfo> with C<OpenCL::GL_MIPMAP_LEVEL> and returns the result.
1561		1778
1562	=for gengetinfo end gl_texture	1779	=for gengetinfo end gl_texture
1563		1780
1564	=back	1781	=back
1565		1782
…		…
1575		1792
1576	=for gengetinfo begin sampler	1793	=for gengetinfo begin sampler
1577		1794
1578	=item $uint = $sampler->reference_count	1795	=item $uint = $sampler->reference_count
1579		1796
1580	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_REFERENCE_COUNT> and returns the result.	1797	Calls C<clGetSamplerInfo> with C<OpenCL::SAMPLER_REFERENCE_COUNT> and returns the result.
1581		1798
1582	=item $ctx = $sampler->context	1799	=item $ctx = $sampler->context
1583		1800
1584	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_CONTEXT> and returns the result.	1801	Calls C<clGetSamplerInfo> with C<OpenCL::SAMPLER_CONTEXT> and returns the result.
1585		1802
1586	=item $addressing_mode = $sampler->normalized_coords	1803	=item $addressing_mode = $sampler->normalized_coords
1587		1804
1588	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_NORMALIZED_COORDS> and returns the result.	1805	Calls C<clGetSamplerInfo> with C<OpenCL::SAMPLER_NORMALIZED_COORDS> and returns the result.
1589		1806
1590	=item $filter_mode = $sampler->addressing_mode	1807	=item $filter_mode = $sampler->addressing_mode
1591		1808
1592	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_ADDRESSING_MODE> and returns the result.	1809	Calls C<clGetSamplerInfo> with C<OpenCL::SAMPLER_ADDRESSING_MODE> and returns the result.
1593		1810
1594	=item $boolean = $sampler->filter_mode	1811	=item $boolean = $sampler->filter_mode
1595		1812
1596	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_FILTER_MODE> and returns the result.	1813	Calls C<clGetSamplerInfo> with C<OpenCL::SAMPLER_FILTER_MODE> and returns the result.
1597		1814
1598	=for gengetinfo end sampler	1815	=for gengetinfo end sampler
1599		1816
1600	=back	1817	=back
1601		1818
…		…
1619	not so. So best make sure you don't pass in invalid values.	1836	not so. So best make sure you don't pass in invalid values.
1620		1837
1621	Some implementations fail with C<OpenCL::INVALID_BINARY> when the	1838	Some implementations fail with C<OpenCL::INVALID_BINARY> when the
1622	compilation state is successful but some later stage fails.	1839	compilation state is successful but some later stage fails.
1623		1840
		1841	options: C<-D name>, C<-D name=definition>, C<-I dir>,
		1842	C<-cl-single-precision-constant>, C<-cl-denorms-are-zero>,
		1843	C<-cl-fp32-correctly-rounded-divide-sqrt>, C<-cl-opt-disable>,
		1844	C<-cl-mad-enable>, C<-cl-no-signed-zeros>, C<-cl-unsafe-math-optimizations>,
		1845	C<-cl-finite-math-only>, C<-cl-fast-relaxed-math>,
		1846	C<-w>, C<-Werror>, C<-cl-std=CL1.1/CL1.2>, C<-cl-kernel-arg-info>,
		1847	C<-create-library>, C<-enable-link-options>.
		1848
		1849	build_status: OpenCL::BUILD_SUCCESS, OpenCL::BUILD_NONE,
		1850	OpenCL::BUILD_ERROR, OpenCL::BUILD_IN_PROGRESS.
		1851
1624	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clBuildProgram.html>	1852	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clBuildProgram.html>
1625		1853
1626	=item $program->build_async (\@devices = undef, $options = "", $cb->($program) = undef)	1854	=item $program->build_async (\@devices = undef, $options = "", $cb->($program) = undef)
1627		1855
1628	Similar to C<< ->build >>, except it starts a thread, and never fails (you	1856	Similar to C<< ->build >>, except it starts a thread, and never fails (you
1629	need to check the compilation status form the callback, or by polling).	1857	need to check the compilation status form the callback, or by polling).
1630		1858
		1859	=item $program->compile (\@devices = undef, $options = "", \%headers = undef, $cb->($program) = undef)
		1860
		1861	Compiles the given program for the given devices (or all devices if
		1862	undef). If C<$headers> is given, it must be a hashref with include name =>
		1863	OpenCL::Program pairs.
		1864
		1865	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCompileProgram.html>
		1866
1631	=item $packed_value = $program->build_info ($device, $name)	1867	=item $packed_value = $program->build_info ($device, $name)
1632		1868
1633	Similar to C<< $platform->info >>, but returns build info for a previous	1869	Similar to C<< $platform->info >>, but returns build info for a previous
1634	build attempt for the given device.	1870	build attempt for the given device.
1635		1871
		1872	binary_type: OpenCL::PROGRAM_BINARY_TYPE_NONE,
		1873	OpenCL::PROGRAM_BINARY_TYPE_COMPILED_OBJECT,
		1874	OpenCL::PROGRAM_BINARY_TYPE_LIBRARY,
		1875	OpenCL::PROGRAM_BINARY_TYPE_EXECUTABLE.
		1876
1636	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetBuildInfo.html>	1877	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetBuildInfo.html>
1637		1878
1638	=item $kernel = $program->kernel ($function_name)	1879	=item $kernel = $program->kernel ($function_name)
1639		1880
1640	Creates an OpenCL::Kernel object out of the named C<__kernel> function in	1881	Creates an OpenCL::Kernel object out of the named C<__kernel> function in
…		…
1650		1891
1651	=for gengetinfo begin program_build	1892	=for gengetinfo begin program_build
1652		1893
1653	=item $build_status = $program->build_status ($device)	1894	=item $build_status = $program->build_status ($device)
1654		1895
1655	Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_STATUS> and returns the result.	1896	Calls C<clGetProgramBuildInfo> with C<OpenCL::PROGRAM_BUILD_STATUS> and returns the result.
1656		1897
1657	=item $string = $program->build_options ($device)	1898	=item $string = $program->build_options ($device)
1658		1899
1659	Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_OPTIONS> and returns the result.	1900	Calls C<clGetProgramBuildInfo> with C<OpenCL::PROGRAM_BUILD_OPTIONS> and returns the result.
1660		1901
1661	=item $string = $program->build_log ($device)	1902	=item $string = $program->build_log ($device)
1662		1903
1663	Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_LOG> and returns the result.	1904	Calls C<clGetProgramBuildInfo> with C<OpenCL::PROGRAM_BUILD_LOG> and returns the result.
		1905
		1906	=item $binary_type = $program->binary_type ($device)
		1907
		1908	Calls C<clGetProgramBuildInfo> with C<OpenCL::PROGRAM_BINARY_TYPE> and returns the result.
1664		1909
1665	=for gengetinfo end program_build	1910	=for gengetinfo end program_build
1666		1911
1667	=item $packed_value = $program->info ($name)	1912	=item $packed_value = $program->info ($name)
1668		1913
…		…
1672		1917
1673	=for gengetinfo begin program	1918	=for gengetinfo begin program
1674		1919
1675	=item $uint = $program->reference_count	1920	=item $uint = $program->reference_count
1676		1921
1677	Calls C<clGetProgramInfo> with C<CL_PROGRAM_REFERENCE_COUNT> and returns the result.	1922	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_REFERENCE_COUNT> and returns the result.
1678		1923
1679	=item $ctx = $program->context	1924	=item $ctx = $program->context
1680		1925
1681	Calls C<clGetProgramInfo> with C<CL_PROGRAM_CONTEXT> and returns the result.	1926	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_CONTEXT> and returns the result.
1682		1927
1683	=item $uint = $program->num_devices	1928	=item $uint = $program->num_devices
1684		1929
1685	Calls C<clGetProgramInfo> with C<CL_PROGRAM_NUM_DEVICES> and returns the result.	1930	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_NUM_DEVICES> and returns the result.
1686		1931
1687	=item @devices = $program->devices	1932	=item @devices = $program->devices
1688		1933
1689	Calls C<clGetProgramInfo> with C<CL_PROGRAM_DEVICES> and returns the result.	1934	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_DEVICES> and returns the result.
1690		1935
1691	=item $string = $program->source	1936	=item $string = $program->source
1692		1937
1693	Calls C<clGetProgramInfo> with C<CL_PROGRAM_SOURCE> and returns the result.	1938	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_SOURCE> and returns the result.
1694		1939
1695	=item @ints = $program->binary_sizes	1940	=item @ints = $program->binary_sizes
1696		1941
1697	Calls C<clGetProgramInfo> with C<CL_PROGRAM_BINARY_SIZES> and returns the result.	1942	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_BINARY_SIZES> and returns the result.
1698		1943
1699	=for gengetinfo end program	1944	=for gengetinfo end program
1700		1945
1701	=item @blobs = $program->binaries	1946	=item @blobs = $program->binaries
1702		1947
…		…
1723		1968
1724	=for gengetinfo begin kernel	1969	=for gengetinfo begin kernel
1725		1970
1726	=item $string = $kernel->function_name	1971	=item $string = $kernel->function_name
1727		1972
1728	Calls C<clGetKernelInfo> with C<CL_KERNEL_FUNCTION_NAME> and returns the result.	1973	Calls C<clGetKernelInfo> with C<OpenCL::KERNEL_FUNCTION_NAME> and returns the result.
1729		1974
1730	=item $uint = $kernel->num_args	1975	=item $uint = $kernel->num_args
1731		1976
1732	Calls C<clGetKernelInfo> with C<CL_KERNEL_NUM_ARGS> and returns the result.	1977	Calls C<clGetKernelInfo> with C<OpenCL::KERNEL_NUM_ARGS> and returns the result.
1733		1978
1734	=item $uint = $kernel->reference_count	1979	=item $uint = $kernel->reference_count
1735		1980
1736	Calls C<clGetKernelInfo> with C<CL_KERNEL_REFERENCE_COUNT> and returns the result.	1981	Calls C<clGetKernelInfo> with C<OpenCL::KERNEL_REFERENCE_COUNT> and returns the result.
1737		1982
1738	=item $ctx = $kernel->context	1983	=item $ctx = $kernel->context
1739		1984
1740	Calls C<clGetKernelInfo> with C<CL_KERNEL_CONTEXT> and returns the result.	1985	Calls C<clGetKernelInfo> with C<OpenCL::KERNEL_CONTEXT> and returns the result.
1741		1986
1742	=item $program = $kernel->program	1987	=item $program = $kernel->program
1743		1988
1744	Calls C<clGetKernelInfo> with C<CL_KERNEL_PROGRAM> and returns the result.	1989	Calls C<clGetKernelInfo> with C<OpenCL::KERNEL_PROGRAM> and returns the result.
1745		1990
1746	=for gengetinfo end kernel	1991	=for gengetinfo end kernel
1747		1992
1748	=item $packed_value = $kernel->work_group_info ($device, $name)	1993	=item $packed_value = $kernel->work_group_info ($device, $name)
1749		1994
1750	See C<< $platform->info >> for details.	1995	See C<< $platform->info >> for details.
1751		1996
1752	The reason this method is not called C<info> is that there already is an
1753	C<< ->info >> method.
1754
1755	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetKernelWorkGroupInfo.html>	1997	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetKernelWorkGroupInfo.html>
1756		1998
1757	=for gengetinfo begin kernel_work_group	1999	=for gengetinfo begin kernel_work_group
1758		2000
1759	=item $int = $kernel->work_group_size ($device)	2001	=item $int = $kernel->work_group_size ($device)
1760		2002
1761	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_WORK_GROUP_SIZE> and returns the result.	2003	Calls C<clGetKernelWorkGroupInfo> with C<OpenCL::KERNEL_WORK_GROUP_SIZE> and returns the result.
1762		2004
1763	=item @ints = $kernel->compile_work_group_size ($device)	2005	=item @ints = $kernel->compile_work_group_size ($device)
1764		2006
1765	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_COMPILE_WORK_GROUP_SIZE> and returns the result.	2007	Calls C<clGetKernelWorkGroupInfo> with C<OpenCL::KERNEL_COMPILE_WORK_GROUP_SIZE> and returns the result.
1766		2008
1767	=item $ulong = $kernel->local_mem_size ($device)	2009	=item $ulong = $kernel->local_mem_size ($device)
1768		2010
1769	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_LOCAL_MEM_SIZE> and returns the result.	2011	Calls C<clGetKernelWorkGroupInfo> with C<OpenCL::KERNEL_LOCAL_MEM_SIZE> and returns the result.
1770		2012
1771	=item $int = $kernel->preferred_work_group_size_multiple ($device)	2013	=item $int = $kernel->preferred_work_group_size_multiple ($device)
1772		2014
1773	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE> and returns the result.	2015	Calls C<clGetKernelWorkGroupInfo> with C<OpenCL::KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE> and returns the result.
1774		2016
1775	=item $ulong = $kernel->private_mem_size ($device)	2017	=item $ulong = $kernel->private_mem_size ($device)
1776		2018
1777	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PRIVATE_MEM_SIZE> and returns the result.	2019	Calls C<clGetKernelWorkGroupInfo> with C<OpenCL::KERNEL_PRIVATE_MEM_SIZE> and returns the result.
1778		2020
1779	=for gengetinfo end kernel_work_group	2021	=for gengetinfo end kernel_work_group
		2022
		2023	=item $packed_value = $kernel->arg_info ($idx, $name)
		2024
		2025	See C<< $platform->info >> for details.
		2026
		2027	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clGetKernelArgInfo.html>
		2028
		2029	=for gengetinfo begin kernel_arg
		2030
		2031	=item $kernel_arg_address_qualifier = $kernel->arg_address_qualifier ($idx)
		2032
		2033	Calls C<clGetKernelArgInfo> with C<OpenCL::KERNEL_ARG_ADDRESS_QUALIFIER> and returns the result.
		2034
		2035	=item $kernel_arg_access_qualifier = $kernel->arg_access_qualifier ($idx)
		2036
		2037	Calls C<clGetKernelArgInfo> with C<OpenCL::KERNEL_ARG_ACCESS_QUALIFIER> and returns the result.
		2038
		2039	=item $string = $kernel->arg_type_name ($idx)
		2040
		2041	Calls C<clGetKernelArgInfo> with C<OpenCL::KERNEL_ARG_TYPE_NAME> and returns the result.
		2042
		2043	=item $kernel_arg_type_qualifier = $kernel->arg_type_qualifier ($idx)
		2044
		2045	Calls C<clGetKernelArgInfo> with C<OpenCL::KERNEL_ARG_TYPE_QUALIFIER> and returns the result.
		2046
		2047	=item $string = $kernel->arg_name ($idx)
		2048
		2049	Calls C<clGetKernelArgInfo> with C<OpenCL::KERNEL_ARG_NAME> and returns the result.
		2050
		2051	=for gengetinfo end kernel_arg
1780		2052
1781	=item $kernel->setf ($format, ...)	2053	=item $kernel->setf ($format, ...)
1782		2054
1783	Sets the arguments of a kernel. Since OpenCL 1.1 doesn't have a generic	2055	Sets the arguments of a kernel. Since OpenCL 1.1 doesn't have a generic
1784	way to set arguments (and with OpenCL 1.2 it might be rather slow), you	2056	way to set arguments (and with OpenCL 1.2 it might be rather slow), you
…		…
1896		2168
1897	=for gengetinfo begin event	2169	=for gengetinfo begin event
1898		2170
1899	=item $queue = $event->command_queue	2171	=item $queue = $event->command_queue
1900		2172
1901	Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_QUEUE> and returns the result.	2173	Calls C<clGetEventInfo> with C<OpenCL::EVENT_COMMAND_QUEUE> and returns the result.
1902		2174
1903	=item $command_type = $event->command_type	2175	=item $command_type = $event->command_type
1904		2176
1905	Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_TYPE> and returns the result.	2177	Calls C<clGetEventInfo> with C<OpenCL::EVENT_COMMAND_TYPE> and returns the result.
1906		2178
1907	=item $uint = $event->reference_count	2179	=item $uint = $event->reference_count
1908		2180
1909	Calls C<clGetEventInfo> with C<CL_EVENT_REFERENCE_COUNT> and returns the result.	2181	Calls C<clGetEventInfo> with C<OpenCL::EVENT_REFERENCE_COUNT> and returns the result.
1910		2182
1911	=item $uint = $event->command_execution_status	2183	=item $uint = $event->command_execution_status
1912		2184
1913	Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_EXECUTION_STATUS> and returns the result.	2185	Calls C<clGetEventInfo> with C<OpenCL::EVENT_COMMAND_EXECUTION_STATUS> and returns the result.
1914		2186
1915	=item $ctx = $event->context	2187	=item $ctx = $event->context
1916		2188
1917	Calls C<clGetEventInfo> with C<CL_EVENT_CONTEXT> and returns the result.	2189	Calls C<clGetEventInfo> with C<OpenCL::EVENT_CONTEXT> and returns the result.
1918		2190
1919	=for gengetinfo end event	2191	=for gengetinfo end event
1920		2192
1921	=item $packed_value = $ev->profiling_info ($name)	2193	=item $packed_value = $ev->profiling_info ($name)
1922		2194
…		…
1929		2201
1930	=for gengetinfo begin profiling	2202	=for gengetinfo begin profiling
1931		2203
1932	=item $ulong = $event->profiling_command_queued	2204	=item $ulong = $event->profiling_command_queued
1933		2205
1934	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_QUEUED> and returns the result.	2206	Calls C<clGetEventProfilingInfo> with C<OpenCL::PROFILING_COMMAND_QUEUED> and returns the result.
1935		2207
1936	=item $ulong = $event->profiling_command_submit	2208	=item $ulong = $event->profiling_command_submit
1937		2209
1938	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_SUBMIT> and returns the result.	2210	Calls C<clGetEventProfilingInfo> with C<OpenCL::PROFILING_COMMAND_SUBMIT> and returns the result.
1939		2211
1940	=item $ulong = $event->profiling_command_start	2212	=item $ulong = $event->profiling_command_start
1941		2213
1942	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_START> and returns the result.	2214	Calls C<clGetEventProfilingInfo> with C<OpenCL::PROFILING_COMMAND_START> and returns the result.
1943		2215
1944	=item $ulong = $event->profiling_command_end	2216	=item $ulong = $event->profiling_command_end
1945		2217
1946	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_END> and returns the result.	2218	Calls C<clGetEventProfilingInfo> with C<OpenCL::PROFILING_COMMAND_END> and returns the result.
1947		2219
1948	=for gengetinfo end profiling	2220	=for gengetinfo end profiling
1949		2221
1950	=back	2222	=back
1951		2223
…		…
1957		2229
1958	=item $ev->set_status ($execution_status)	2230	=item $ev->set_status ($execution_status)
1959		2231
1960	Sets the execution status of the user event. Can only be called once,	2232	Sets the execution status of the user event. Can only be called once,
1961	either with OpenCL::COMPLETE or a negative number as status.	2233	either with OpenCL::COMPLETE or a negative number as status.
		2234
		2235	execution_status: OpenCL::COMPLETE or a negative integer.
1962		2236
1963	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetUserEventStatus.html>	2237	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetUserEventStatus.html>
1964		2238
1965	=back	2239	=back
1966		2240
…		…
2020		2294
2021	Returns the size of the mapped area, in bytes. Same as C<length $$mapped>.	2295	Returns the size of the mapped area, in bytes. Same as C<length $$mapped>.
2022		2296
2023	=item $ptr = $mapped->ptr	2297	=item $ptr = $mapped->ptr
2024		2298
2025	Returns the raw memory address of the mapped area - same as C<$mapped+0>.	2299	Returns the raw memory address of the mapped area.
2026		2300
2027	=item $mapped->set ($offset, $data)	2301	=item $mapped->set ($offset, $data)
2028		2302
2029	Replaces the data at the given C<$offset> in the memory area by the new	2303	Replaces the data at the given C<$offset> in the memory area by the new
2030	C<$data>. This method is safer but slower than direct manipulation of	2304	C<$data>. This method is safer than direct manipulation of C<$mapped>
2031	C<$$mapped> with substr.	2305	because it does bounds-checking, but also slower.
2032		2306
2033	=item $data = $mapped->get ($offset, $length)	2307	=item $data = $mapped->get ($offset, $length)
2034		2308
2035	Returns (without copying) a scalar representing the data at the given	2309	Returns (without copying) a scalar representing the data at the given
2036	C<$offset> and C<$length> in the mapped memory area. This is the same as	2310	C<$offset> and C<$length> in the mapped memory area. This is the same as
2037	the following substr, except much slower:	2311	the following substr, except much slower;
2038		2312
2039	$data = substr $$mapped, $offset, $length	2313	$data = substr $$mapped, $offset, $length
2040		2314
2041	#TODO: really?
2042
2043	=cut	2315	=cut
2044		2316
2045	sub get {	2317	sub OpenCL::Mapped::get {
2046	substr ${$_[0]}, $_[1], $_[2]	2318	substr ${$_[0]}, $_[1], $_[2]
2047	}	2319	}
2048		2320
2049	=back	2321	=back
2050		2322

Diff Legend

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

Comparing OpenCL/OpenCL.pm (file contents): Revision 1.67 by root, Tue May 1 22:04:56 2012 UTC vs. Revision 1.80 by root, Sat May 5 13:55:59 2012 UTC

Diff Legend

Comparing OpenCL/OpenCL.pm (file contents):
Revision 1.67 by root, Tue May 1 22:04:56 2012 UTC vs.
Revision 1.80 by root, Sat May 5 13:55:59 2012 UTC