[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.88 by root, Tue Oct 22 17:25:38 2013 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 also download it
218	L<http://cvs.schmorp.de/OpenCL/examples/juliaflight>.	219	from L<http://cvs.schmorp.de/OpenCL/examples/juliaflight>.
219		220
220	use OpenGL ":all";	221	use OpenGL ":all";
221	use OpenCL;	222	use OpenCL;
222		223
223	my $S = $ARGV[0] \|\| 256; # window/texture size, smaller is faster	224	my $S = $ARGV[0] \|\| 256; # window/texture size, smaller is faster
…		…
231	# find and use the first opencl device that let's us get a shared opengl context	232	# find and use the first opencl device that let's us get a shared opengl context
232	my $platform;	233	my $platform;
233	my $dev;	234	my $dev;
234	my $ctx;	235	my $ctx;
235		236
		237	sub get_context {
236	for (OpenCL::platforms) {	238	for (OpenCL::platforms) {
237	$platform = $_;	239	$platform = $_;
238	for ($platform->devices) {	240	for ($platform->devices) {
239	$dev = $_;	241	$dev = $_;
240	$ctx = $platform->context ([OpenCL::GLX_DISPLAY_KHR, undef, OpenCL::GL_CONTEXT_KHR, undef], [$dev])	242	$ctx = eval { $platform->context ([OpenCL::GLX_DISPLAY_KHR, undef, OpenCL::GL_CONTEXT_KHR, undef], [$dev]) }
241	and last;	243	and return;
		244	}
242	}	245	}
		246
		247	die "cannot find suitable OpenCL device\n";
243	}	248	}
244		249
245	$ctx	250	get_context;
246	or die "cannot find suitable OpenCL device\n";
247		251
248	my $queue = $ctx->queue ($dev);	252	my $queue = $ctx->queue ($dev);
249		253
250	# now attach an opencl image2d object to the opengl texture	254	# now attach an opencl image2d object to the opengl texture
251	my $tex = $ctx->gl_texture2d (OpenCL::MEM_WRITE_ONLY, GL_TEXTURE_2D, 0, $texid);	255	my $tex = $ctx->gl_texture2d (OpenCL::MEM_WRITE_ONLY, GL_TEXTURE_2D, 0, $texid);
…		…
320	To use a texture, you would modify the above example by creating an	324	To use a texture, you would modify the above example by creating an
321	OpenCL::Image manually instead of deriving it from a texture:	325	OpenCL::Image manually instead of deriving it from a texture:
322		326
323	my $tex = $ctx->image2d (OpenCL::MEM_WRITE_ONLY, OpenCL::RGBA, OpenCL::UNORM_INT8, $S, $S);	327	my $tex = $ctx->image2d (OpenCL::MEM_WRITE_ONLY, OpenCL::RGBA, OpenCL::UNORM_INT8, $S, $S);
324		328
325	And in the darw loop, intead of acquire_gl_objects/release_gl_objects, you	329	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:	330	would read the image2d after the kernel has written it:
327		331
328	$queue->read_image ($tex, 0, 0, 0, 0, $S, $S, 1, 0, 0, my $data);	332	$queue->read_image ($tex, 0, 0, 0, 0, $S, $S, 1, 0, 0, my $data);
329		333
330	And then you would upload the pixel data to the texture (or use glDrawPixels):	334	And then you would upload the pixel data to the texture (or use glDrawPixels):
331		335
332	glTexSubImage2D_s GL_TEXTURE_2D, 0, 0, 0, $S, $S, GL_RGBA, GL_UNSIGNED_BYTE, $data;	336	glTexSubImage2D_s GL_TEXTURE_2D, 0, 0, 0, $S, $S, GL_RGBA, GL_UNSIGNED_BYTE, $data;
333		337
334	The fully modified example can be found at	338	The fully modified example can be found at
335	L<http://cvs.schmorp.de/OpenCL/examples/juliaflight-nosharing>.	339	L<http://cvs.schmorp.de/OpenCL/examples/juliaflight-nosharing>.
		340
		341	=head2 Julia sets look soooo 80ies.
		342
		343	Then colour them differently, e.g. using orbit traps! Replace the loop and
		344	colour calculation from the previous examples by this:
		345
		346	float2 dm = (float2)(1.f, 1.f);
		347
		348	for (int i = 0; i < 25; ++i)
		349	{
		350	z = (float2)(z.x * z.x - z.y * z.y, 2.f * z.x * z.y) + c;
		351	dm = fmin (dm, (float2)(fabs (dot (z, z) - 1.f), fabs (z.x - 1.f)));
		352	}
		353
		354	float3 colour = (float3)(dm.x * dm.y, dm.x * dm.y, dm.x);
		355
		356	Also try C<-10.f> instead of C<-1.f>.
336		357
337	=head1 DOCUMENTATION	358	=head1 DOCUMENTATION
338		359
339	=head2 BASIC CONVENTIONS	360	=head2 BASIC CONVENTIONS
340		361
…		…
370		391
371	=item * When enqueuing commands, if the enqueue method is called in void	392	=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	393	context, no event is created. In all other contexts an event is returned
373	by the method.	394	by the method.
374		395
375	=item * This module expects all functions to return C<CL_SUCCESS>. If any	396	=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	397	other status is returned the function will throw an exception, so you
377	don't normally have to to any error checking.	398	don't normally have to to any error checking.
378		399
379	=back	400	=back
		401
		402	=head2 CONSTANTS
		403
		404	All C<CL_xxx> constants that this module supports are always available
		405	in the C<OpenCL> namespace as C<OpenCL::xxx> (i.e. without the C<CL_>
		406	prefix). Constants which are not defined in the header files used during
		407	compilation, or otherwise are not available, will have the value C<0> (in
		408	some cases, this will make them indistinguishable from real constants,
		409	sorry).
		410
		411	The latest version of this module knows and exports the constants
		412	listed in L<http://cvs.schmorp.de/OpenCL/constiv.h>.
		413
		414	=head2 OPENCL 1.1 VS. OPENCL 1.2
		415
		416	This module supports both OpenCL version 1.1 and 1.2, although the OpenCL
		417	1.2 interface hasn't been tested much for lack of availability of an
		418	actual implementation.
		419
		420	Every function or method in this manual page that interfaces to a
		421	particular OpenCL function has a link to the its C manual page.
		422
		423	If the link contains a F<1.1>, then this function is an OpenCL 1.1
		424	function. Most but not all also exist in OpenCL 1.2, and this module
		425	tries to emulate the missing ones for you, when told to do so at
		426	compiletime. You can check whether a function was removed in OpenCL 1.2 by
		427	replacing the F<1.1> component in the URL by F<1.2>.
		428
		429	If the link contains a F<1.2>, then this is a OpenCL 1.2-only
		430	function. Even if the module was compiled with OpenCL 1.2 header files
		431	and has an 1.2 OpenCL library, calling such a function on a platform that
		432	doesn't implement 1.2 causes undefined behaviour, usually a crash (But
		433	this is not guaranteed).
		434
		435	You can find out whether this module was compiled to prefer 1.1
		436	functionality by ooking at C<OpenCL::PREFER_1_1> - if it is true, then
		437	1.1 functions generally are implemented using 1.1 OpenCL functions. If it
		438	is false, then 1.1 functions missing from 1.2 are emulated by calling 1.2
		439	fucntions.
		440
		441	This is a somewhat sorry state of affairs, but the Khronos group choose to
		442	make every release of OpenCL source and binary incompatible with previous
		443	releases.
380		444
381	=head2 PERL AND OPENCL TYPES	445	=head2 PERL AND OPENCL TYPES
382		446
383	This handy(?) table lists OpenCL types and their perl, PDL and pack/unpack	447	This handy(?) table lists OpenCL types and their perl, PDL and pack/unpack
384	format equivalents:	448	format equivalents:
…		…
416	OpenCL can generate a number of (potentially) asynchronous events, for	480	OpenCL can generate a number of (potentially) asynchronous events, for
417	example, after compiling a program, to signal a context-related error or,	481	example, after compiling a program, to signal a context-related error or,
418	perhaps most important, to signal completion of queued jobs (by setting	482	perhaps most important, to signal completion of queued jobs (by setting
419	callbacks on OpenCL::Event objects).	483	callbacks on OpenCL::Event objects).
420		484
		485	The OpenCL module converts all these callbacks into events - you can
		486	still register callbacks, but they are not executed when your OpenCL
		487	implementation calls the actual callback, but only later. Therefore, none
		488	of the limitations of OpenCL callbacks apply to the perl implementation:
		489	it is perfectly safe to make blocking operations from event callbacks, and
		490	enqueued operations don't need to be flushed.
		491
421	To facilitate this, this module maintains an event queue - each	492	To facilitate this, this module maintains an event queue - each
422	time an asynchronous event happens, it is queued, and perl will be	493	time an asynchronous event happens, it is queued, and perl will be
423	interrupted. This is implemented via the L<Async::Interrupt> module. In	494	interrupted. This is implemented via the L<Async::Interrupt> module. In
424	addition, this module has L<AnyEvent> support, so it can seamlessly	495	addition, this module has L<AnyEvent> support, so it can seamlessly
425	integrate itself into many event loops.	496	integrate itself into many event loops.
426		497
427	Since this module is a bit hard to understand, here are some case examples:	498	Since L<Async::Interrupt> is a bit hard to understand, here are some case examples:
428		499
429	=head3 Don't use callbacks.	500	=head3 Don't use callbacks.
430		501
431	When your program never uses any callbacks, then there will never be any	502	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	503	notifications you need to take care of, and therefore no need to worry
…		…
529	use Async::Interrupt ();	600	use Async::Interrupt ();
530		601
531	our $POLL_FUNC; # set by XS	602	our $POLL_FUNC; # set by XS
532		603
533	BEGIN {	604	BEGIN {
534	our $VERSION = '0.98';	605	our $VERSION = '1.01';
535		606
536	require XSLoader;	607	require XSLoader;
537	XSLoader::load (__PACKAGE__, $VERSION);	608	XSLoader::load (__PACKAGE__, $VERSION);
538		609
539	@OpenCL::Platform::ISA =	610	@OpenCL::Platform::ISA =
…		…
544	@OpenCL::Sampler::ISA =	615	@OpenCL::Sampler::ISA =
545	@OpenCL::Program::ISA =	616	@OpenCL::Program::ISA =
546	@OpenCL::Kernel::ISA =	617	@OpenCL::Kernel::ISA =
547	@OpenCL::Event::ISA = OpenCL::Object::;	618	@OpenCL::Event::ISA = OpenCL::Object::;
548		619
		620	@OpenCL::SubDevice::ISA = OpenCL::Device::;
		621
549	@OpenCL::Buffer::ISA =	622	@OpenCL::Buffer::ISA =
550	@OpenCL::Image::ISA = OpenCL::Memory::;	623	@OpenCL::Image::ISA = OpenCL::Memory::;
551		624
552	@OpenCL::BufferObj::ISA = OpenCL::Buffer::;	625	@OpenCL::BufferObj::ISA = OpenCL::Buffer::;
553		626
…		…
573	The last error returned by a function - it's only valid after an error occured	646	The last error returned by a function - it's only valid after an error occured
574	and before calling another OpenCL function.	647	and before calling another OpenCL function.
575		648
576	=item $str = OpenCL::err2str [$errval]	649	=item $str = OpenCL::err2str [$errval]
577		650
578	Converts an error value into a human readable string. IF no error value is	651	Converts an error value into a human readable string. If no error value is
579	given, then the last error will be used (as returned by OpenCL::errno).	652	given, then the last error will be used (as returned by OpenCL::errno).
		653
		654	The latest version of this module knows the error constants
		655	listed in L<http://cvs.schmorp.de/OpenCL/errstr.h>.
580		656
581	=item $str = OpenCL::enum2str $enum	657	=item $str = OpenCL::enum2str $enum
582		658
583	Converts most enum values (of parameter names, image format constants,	659	Converts most enum values (of parameter names, image format constants,
584	object types, addressing and filter modes, command types etc.) into a	660	object types, addressing and filter modes, command types etc.) into a
585	human readable string. When confronted with some random integer it can be	661	human readable string. When confronted with some random integer it can be
586	very helpful to pass it through this function to maybe get some readable	662	very helpful to pass it through this function to maybe get some readable
587	string out of it.	663	string out of it.
588		664
		665	The latest version of this module knows the enumaration constants
		666	listed in L<http://cvs.schmorp.de/OpenCL/enumstr.h>.
		667
589	=item @platforms = OpenCL::platforms	668	=item @platforms = OpenCL::platforms
590		669
591	Returns all available OpenCL::Platform objects.	670	Returns all available OpenCL::Platform objects.
592		671
593	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformIDs.html>	672	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetPlatformIDs.html>
594		673
595	=item $ctx = OpenCL::context_from_type $properties, $type = OpenCL::DEVICE_TYPE_DEFAULT, $callback->($err, $pvt) = $print_stderr	674	=item $ctx = OpenCL::context_from_type $properties, $type = OpenCL::DEVICE_TYPE_DEFAULT, $callback->($err, $pvt) = $print_stderr
596		675
597	Tries to create a context from a default device and platform type - never worked for me.	676	Tries to create a context from a default device and platform type - never worked for me.
		677	Consider using C<< $platform->context_from_type >> instead.
		678
		679	type: OpenCL::DEVICE_TYPE_DEFAULT, OpenCL::DEVICE_TYPE_CPU, OpenCL::DEVICE_TYPE_GPU,
		680	OpenCL::DEVICE_TYPE_ACCELERATOR, OpenCL::DEVICE_TYPE_CUSTOM, OpenCL::DEVICE_TYPE_ALL.
598		681
599	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>	682	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>
600		683
601	=item $ctx = OpenCL::context $properties, \@devices, $callback->($err, $pvt) = $print_stderr)	684	=item $ctx = OpenCL::context $properties, \@devices, $callback->($err, $pvt) = $print_stderr)
602		685
603	Create a new OpenCL::Context object using the given device object(s). This	686	Create a new OpenCL::Context object using the given device object(s).
604	function isn't implemented yet, use C<< $platform->context >> instead.	687	Consider using C<< $platform->context >> instead.
605		688
606	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>	689	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>
607		690
608	=item OpenCL::wait_for_events $wait_events...	691	=item OpenCL::wait_for_events $wait_events...
609		692
…		…
690	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>	773	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContextFromType.html>
691		774
692	=item $ctx = $platform->context ($properties, \@devices, $callback->($err, $pvt) = $print_stderr)	775	=item $ctx = $platform->context ($properties, \@devices, $callback->($err, $pvt) = $print_stderr)
693		776
694	Create a new OpenCL::Context object using the given device object(s)- a	777	Create a new OpenCL::Context object using the given device object(s)- a
695	CL_CONTEXT_PLATFORM property is supplied automatically.	778	OpenCL::CONTEXT_PLATFORM property is supplied automatically.
696		779
697	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>	780	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateContext.html>
698		781
699	=item $packed_value = $platform->info ($name)	782	=item $packed_value = $platform->info ($name)
700		783
…		…
716		799
717	=for gengetinfo begin platform	800	=for gengetinfo begin platform
718		801
719	=item $string = $platform->profile	802	=item $string = $platform->profile
720		803
721	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_PROFILE> and returns the result.	804	Calls C<clGetPlatformInfo> with C<OpenCL::PLATFORM_PROFILE> and returns the result.
722		805
723	=item $string = $platform->version	806	=item $string = $platform->version
724		807
725	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VERSION> and returns the result.	808	Calls C<clGetPlatformInfo> with C<OpenCL::PLATFORM_VERSION> and returns the result.
726		809
727	=item $string = $platform->name	810	=item $string = $platform->name
728		811
729	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_NAME> and returns the result.	812	Calls C<clGetPlatformInfo> with C<OpenCL::PLATFORM_NAME> and returns the result.
730		813
731	=item $string = $platform->vendor	814	=item $string = $platform->vendor
732		815
733	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_VENDOR> and returns the result.	816	Calls C<clGetPlatformInfo> with C<OpenCL::PLATFORM_VENDOR> and returns the result.
734		817
735	=item $string = $platform->extensions	818	=item $string = $platform->extensions
736		819
737	Calls C<clGetPlatformInfo> with C<CL_PLATFORM_EXTENSIONS> and returns the result.	820	Calls C<clGetPlatformInfo> with C<OpenCL::PLATFORM_EXTENSIONS> and returns the result.
738		821
739	=for gengetinfo end platform	822	=for gengetinfo end platform
740		823
741	=back	824	=back
742		825
…		…
746		829
747	=item $packed_value = $device->info ($name)	830	=item $packed_value = $device->info ($name)
748		831
749	See C<< $platform->info >> for details.	832	See C<< $platform->info >> for details.
750		833
		834	type: OpenCL::DEVICE_TYPE_DEFAULT, OpenCL::DEVICE_TYPE_CPU,
		835	OpenCL::DEVICE_TYPE_GPU, OpenCL::DEVICE_TYPE_ACCELERATOR,
		836	OpenCL::DEVICE_TYPE_CUSTOM, OpenCL::DEVICE_TYPE_ALL.
		837
		838	fp_config: OpenCL::FP_DENORM, OpenCL::FP_INF_NAN, OpenCL::FP_ROUND_TO_NEAREST,
		839	OpenCL::FP_ROUND_TO_ZERO, OpenCL::FP_ROUND_TO_INF, OpenCL::FP_FMA,
		840	OpenCL::FP_SOFT_FLOAT, OpenCL::FP_CORRECTLY_ROUNDED_DIVIDE_SQRT.
		841
		842	mem_cache_type: OpenCL::NONE, OpenCL::READ_ONLY_CACHE, OpenCL::READ_WRITE_CACHE.
		843
		844	local_mem_type: OpenCL::LOCAL, OpenCL::GLOBAL.
		845
		846	exec_capabilities: OpenCL::EXEC_KERNEL, OpenCL::EXEC_NATIVE_KERNEL.
		847
		848	command_queue_properties: OpenCL::QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE,
		849	OpenCL::QUEUE_PROFILING_ENABLE.
		850
		851	partition_properties: OpenCL::DEVICE_PARTITION_EQUALLY,
		852	OpenCL::DEVICE_PARTITION_BY_COUNTS, OpenCL::DEVICE_PARTITION_BY_COUNTS_LIST_END,
		853	OpenCL::DEVICE_PARTITION_BY_AFFINITY_DOMAIN.
		854
		855	affinity_domain: OpenCL::DEVICE_AFFINITY_DOMAIN_NUMA,
		856	OpenCL::DEVICE_AFFINITY_DOMAIN_L4_CACHE, OpenCL::DEVICE_AFFINITY_DOMAIN_L3_CACHE,
		857	OpenCL::DEVICE_AFFINITY_DOMAIN_L2_CACHE, OpenCL::DEVICE_AFFINITY_DOMAIN_L1_CACHE,
		858	OpenCL::DEVICE_AFFINITY_DOMAIN_NEXT_PARTITIONABLE.
		859
751	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetDeviceInfo.html>	860	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetDeviceInfo.html>
752		861
		862	=item @devices = $device->sub_devices (\@properties)
		863
		864	Creates OpencL::SubDevice objects by partitioning an existing device.
		865
		866	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateSubDevices.html>
		867
753	=for gengetinfo begin device	868	=for gengetinfo begin device
754		869
755	=item $device_type = $device->type	870	=item $device_type = $device->type
756		871
757	Calls C<clGetDeviceInfo> with C<CL_DEVICE_TYPE> and returns the result.	872	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_TYPE> and returns the result.
758		873
759	=item $uint = $device->vendor_id	874	=item $uint = $device->vendor_id
760		875
761	Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR_ID> and returns the result.	876	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_VENDOR_ID> and returns the result.
762		877
763	=item $uint = $device->max_compute_units	878	=item $uint = $device->max_compute_units
764		879
765	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_COMPUTE_UNITS> and returns the result.	880	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_COMPUTE_UNITS> and returns the result.
766		881
767	=item $uint = $device->max_work_item_dimensions	882	=item $uint = $device->max_work_item_dimensions
768		883
769	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS> and returns the result.	884	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_WORK_ITEM_DIMENSIONS> and returns the result.
770		885
771	=item $int = $device->max_work_group_size	886	=item $int = $device->max_work_group_size
772		887
773	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_GROUP_SIZE> and returns the result.	888	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_WORK_GROUP_SIZE> and returns the result.
774		889
775	=item @ints = $device->max_work_item_sizes	890	=item @ints = $device->max_work_item_sizes
776		891
777	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WORK_ITEM_SIZES> and returns the result.	892	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_WORK_ITEM_SIZES> and returns the result.
778		893
779	=item $uint = $device->preferred_vector_width_char	894	=item $uint = $device->preferred_vector_width_char
780		895
781	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR> and returns the result.	896	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_CHAR> and returns the result.
782		897
783	=item $uint = $device->preferred_vector_width_short	898	=item $uint = $device->preferred_vector_width_short
784		899
785	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT> and returns the result.	900	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_SHORT> and returns the result.
786		901
787	=item $uint = $device->preferred_vector_width_int	902	=item $uint = $device->preferred_vector_width_int
788		903
789	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT> and returns the result.	904	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_INT> and returns the result.
790		905
791	=item $uint = $device->preferred_vector_width_long	906	=item $uint = $device->preferred_vector_width_long
792		907
793	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG> and returns the result.	908	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_LONG> and returns the result.
794		909
795	=item $uint = $device->preferred_vector_width_float	910	=item $uint = $device->preferred_vector_width_float
796		911
797	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT> and returns the result.	912	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT> and returns the result.
798		913
799	=item $uint = $device->preferred_vector_width_double	914	=item $uint = $device->preferred_vector_width_double
800		915
801	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE> and returns the result.	916	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE> and returns the result.
802		917
803	=item $uint = $device->max_clock_frequency	918	=item $uint = $device->max_clock_frequency
804		919
805	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CLOCK_FREQUENCY> and returns the result.	920	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_CLOCK_FREQUENCY> and returns the result.
806		921
807	=item $bitfield = $device->address_bits	922	=item $bitfield = $device->address_bits
808		923
809	Calls C<clGetDeviceInfo> with C<CL_DEVICE_ADDRESS_BITS> and returns the result.	924	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_ADDRESS_BITS> and returns the result.
810		925
811	=item $uint = $device->max_read_image_args	926	=item $uint = $device->max_read_image_args
812		927
813	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_READ_IMAGE_ARGS> and returns the result.	928	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_READ_IMAGE_ARGS> and returns the result.
814		929
815	=item $uint = $device->max_write_image_args	930	=item $uint = $device->max_write_image_args
816		931
817	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_WRITE_IMAGE_ARGS> and returns the result.	932	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_WRITE_IMAGE_ARGS> and returns the result.
818		933
819	=item $ulong = $device->max_mem_alloc_size	934	=item $ulong = $device->max_mem_alloc_size
820		935
821	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_MEM_ALLOC_SIZE> and returns the result.	936	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_MEM_ALLOC_SIZE> and returns the result.
822		937
823	=item $int = $device->image2d_max_width	938	=item $int = $device->image2d_max_width
824		939
825	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_WIDTH> and returns the result.	940	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE2D_MAX_WIDTH> and returns the result.
826		941
827	=item $int = $device->image2d_max_height	942	=item $int = $device->image2d_max_height
828		943
829	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE2D_MAX_HEIGHT> and returns the result.	944	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE2D_MAX_HEIGHT> and returns the result.
830		945
831	=item $int = $device->image3d_max_width	946	=item $int = $device->image3d_max_width
832		947
833	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_WIDTH> and returns the result.	948	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE3D_MAX_WIDTH> and returns the result.
834		949
835	=item $int = $device->image3d_max_height	950	=item $int = $device->image3d_max_height
836		951
837	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_HEIGHT> and returns the result.	952	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE3D_MAX_HEIGHT> and returns the result.
838		953
839	=item $int = $device->image3d_max_depth	954	=item $int = $device->image3d_max_depth
840		955
841	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE3D_MAX_DEPTH> and returns the result.	956	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE3D_MAX_DEPTH> and returns the result.
842		957
843	=item $uint = $device->image_support	958	=item $uint = $device->image_support
844		959
845	Calls C<clGetDeviceInfo> with C<CL_DEVICE_IMAGE_SUPPORT> and returns the result.	960	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_IMAGE_SUPPORT> and returns the result.
846		961
847	=item $int = $device->max_parameter_size	962	=item $int = $device->max_parameter_size
848		963
849	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_PARAMETER_SIZE> and returns the result.	964	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_PARAMETER_SIZE> and returns the result.
850		965
851	=item $uint = $device->max_samplers	966	=item $uint = $device->max_samplers
852		967
853	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_SAMPLERS> and returns the result.	968	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_SAMPLERS> and returns the result.
854		969
855	=item $uint = $device->mem_base_addr_align	970	=item $uint = $device->mem_base_addr_align
856		971
857	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MEM_BASE_ADDR_ALIGN> and returns the result.	972	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MEM_BASE_ADDR_ALIGN> and returns the result.
858		973
859	=item $uint = $device->min_data_type_align_size	974	=item $uint = $device->min_data_type_align_size
860		975
861	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE> and returns the result.	976	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MIN_DATA_TYPE_ALIGN_SIZE> and returns the result.
862		977
863	=item $device_fp_config = $device->single_fp_config	978	=item $device_fp_config = $device->single_fp_config
864		979
865	Calls C<clGetDeviceInfo> with C<CL_DEVICE_SINGLE_FP_CONFIG> and returns the result.	980	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_SINGLE_FP_CONFIG> and returns the result.
866		981
867	=item $device_mem_cache_type = $device->global_mem_cache_type	982	=item $device_mem_cache_type = $device->global_mem_cache_type
868		983
869	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_TYPE> and returns the result.	984	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_GLOBAL_MEM_CACHE_TYPE> and returns the result.
870		985
871	=item $uint = $device->global_mem_cacheline_size	986	=item $uint = $device->global_mem_cacheline_size
872		987
873	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE> and returns the result.	988	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_GLOBAL_MEM_CACHELINE_SIZE> and returns the result.
874		989
875	=item $ulong = $device->global_mem_cache_size	990	=item $ulong = $device->global_mem_cache_size
876		991
877	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_CACHE_SIZE> and returns the result.	992	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_GLOBAL_MEM_CACHE_SIZE> and returns the result.
878		993
879	=item $ulong = $device->global_mem_size	994	=item $ulong = $device->global_mem_size
880		995
881	Calls C<clGetDeviceInfo> with C<CL_DEVICE_GLOBAL_MEM_SIZE> and returns the result.	996	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_GLOBAL_MEM_SIZE> and returns the result.
882		997
883	=item $ulong = $device->max_constant_buffer_size	998	=item $ulong = $device->max_constant_buffer_size
884		999
885	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE> and returns the result.	1000	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_CONSTANT_BUFFER_SIZE> and returns the result.
886		1001
887	=item $uint = $device->max_constant_args	1002	=item $uint = $device->max_constant_args
888		1003
889	Calls C<clGetDeviceInfo> with C<CL_DEVICE_MAX_CONSTANT_ARGS> and returns the result.	1004	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_MAX_CONSTANT_ARGS> and returns the result.
890		1005
891	=item $device_local_mem_type = $device->local_mem_type	1006	=item $device_local_mem_type = $device->local_mem_type
892		1007
893	Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_TYPE> and returns the result.	1008	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_LOCAL_MEM_TYPE> and returns the result.
894		1009
895	=item $ulong = $device->local_mem_size	1010	=item $ulong = $device->local_mem_size
896		1011
897	Calls C<clGetDeviceInfo> with C<CL_DEVICE_LOCAL_MEM_SIZE> and returns the result.	1012	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_LOCAL_MEM_SIZE> and returns the result.
898		1013
899	=item $boolean = $device->error_correction_support	1014	=item $boolean = $device->error_correction_support
900		1015
901	Calls C<clGetDeviceInfo> with C<CL_DEVICE_ERROR_CORRECTION_SUPPORT> and returns the result.	1016	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_ERROR_CORRECTION_SUPPORT> and returns the result.
902		1017
903	=item $int = $device->profiling_timer_resolution	1018	=item $int = $device->profiling_timer_resolution
904		1019
905	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILING_TIMER_RESOLUTION> and returns the result.	1020	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PROFILING_TIMER_RESOLUTION> and returns the result.
906		1021
907	=item $boolean = $device->endian_little	1022	=item $boolean = $device->endian_little
908		1023
909	Calls C<clGetDeviceInfo> with C<CL_DEVICE_ENDIAN_LITTLE> and returns the result.	1024	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_ENDIAN_LITTLE> and returns the result.
910		1025
911	=item $boolean = $device->available	1026	=item $boolean = $device->available
912		1027
913	Calls C<clGetDeviceInfo> with C<CL_DEVICE_AVAILABLE> and returns the result.	1028	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_AVAILABLE> and returns the result.
914		1029
915	=item $boolean = $device->compiler_available	1030	=item $boolean = $device->compiler_available
916		1031
917	Calls C<clGetDeviceInfo> with C<CL_DEVICE_COMPILER_AVAILABLE> and returns the result.	1032	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_COMPILER_AVAILABLE> and returns the result.
918		1033
919	=item $device_exec_capabilities = $device->execution_capabilities	1034	=item $device_exec_capabilities = $device->execution_capabilities
920		1035
921	Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXECUTION_CAPABILITIES> and returns the result.	1036	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_EXECUTION_CAPABILITIES> and returns the result.
922		1037
923	=item $command_queue_properties = $device->properties	1038	=item $command_queue_properties = $device->properties
924		1039
925	Calls C<clGetDeviceInfo> with C<CL_DEVICE_QUEUE_PROPERTIES> and returns the result.	1040	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_QUEUE_PROPERTIES> and returns the result.
926		1041
927	=item $ = $device->platform	1042	=item $ = $device->platform
928		1043
929	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PLATFORM> and returns the result.	1044	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PLATFORM> and returns the result.
930		1045
931	=item $string = $device->name	1046	=item $string = $device->name
932		1047
933	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NAME> and returns the result.	1048	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NAME> and returns the result.
934		1049
935	=item $string = $device->vendor	1050	=item $string = $device->vendor
936		1051
937	Calls C<clGetDeviceInfo> with C<CL_DEVICE_VENDOR> and returns the result.	1052	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_VENDOR> and returns the result.
938		1053
939	=item $string = $device->driver_version	1054	=item $string = $device->driver_version
940		1055
941	Calls C<clGetDeviceInfo> with C<CL_DRIVER_VERSION> and returns the result.	1056	Calls C<clGetDeviceInfo> with C<OpenCL::DRIVER_VERSION> and returns the result.
942		1057
943	=item $string = $device->profile	1058	=item $string = $device->profile
944		1059
945	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PROFILE> and returns the result.	1060	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PROFILE> and returns the result.
946		1061
947	=item $string = $device->version	1062	=item $string = $device->version
948		1063
949	Calls C<clGetDeviceInfo> with C<CL_DEVICE_VERSION> and returns the result.	1064	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_VERSION> and returns the result.
950		1065
951	=item $string = $device->extensions	1066	=item $string = $device->extensions
952		1067
953	Calls C<clGetDeviceInfo> with C<CL_DEVICE_EXTENSIONS> and returns the result.	1068	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_EXTENSIONS> and returns the result.
954		1069
955	=item $uint = $device->preferred_vector_width_half	1070	=item $uint = $device->preferred_vector_width_half
956		1071
957	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF> and returns the result.	1072	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PREFERRED_VECTOR_WIDTH_HALF> and returns the result.
958		1073
959	=item $uint = $device->native_vector_width_char	1074	=item $uint = $device->native_vector_width_char
960		1075
961	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR> and returns the result.	1076	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_CHAR> and returns the result.
962		1077
963	=item $uint = $device->native_vector_width_short	1078	=item $uint = $device->native_vector_width_short
964		1079
965	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT> and returns the result.	1080	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_SHORT> and returns the result.
966		1081
967	=item $uint = $device->native_vector_width_int	1082	=item $uint = $device->native_vector_width_int
968		1083
969	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_INT> and returns the result.	1084	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_INT> and returns the result.
970		1085
971	=item $uint = $device->native_vector_width_long	1086	=item $uint = $device->native_vector_width_long
972		1087
973	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG> and returns the result.	1088	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_LONG> and returns the result.
974		1089
975	=item $uint = $device->native_vector_width_float	1090	=item $uint = $device->native_vector_width_float
976		1091
977	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT> and returns the result.	1092	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_FLOAT> and returns the result.
978		1093
979	=item $uint = $device->native_vector_width_double	1094	=item $uint = $device->native_vector_width_double
980		1095
981	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE> and returns the result.	1096	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE> and returns the result.
982		1097
983	=item $uint = $device->native_vector_width_half	1098	=item $uint = $device->native_vector_width_half
984		1099
985	Calls C<clGetDeviceInfo> with C<CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF> and returns the result.	1100	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_NATIVE_VECTOR_WIDTH_HALF> and returns the result.
986		1101
987	=item $device_fp_config = $device->double_fp_config	1102	=item $device_fp_config = $device->double_fp_config
988		1103
989	Calls C<clGetDeviceInfo> with C<CL_DEVICE_DOUBLE_FP_CONFIG> and returns the result.	1104	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_DOUBLE_FP_CONFIG> and returns the result.
990		1105
991	=item $device_fp_config = $device->half_fp_config	1106	=item $device_fp_config = $device->half_fp_config
992		1107
993	Calls C<clGetDeviceInfo> with C<CL_DEVICE_HALF_FP_CONFIG> and returns the result.	1108	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_HALF_FP_CONFIG> and returns the result.
994		1109
995	=item $boolean = $device->host_unified_memory	1110	=item $boolean = $device->host_unified_memory
996		1111
997	Calls C<clGetDeviceInfo> with C<CL_DEVICE_HOST_UNIFIED_MEMORY> and returns the result.	1112	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_HOST_UNIFIED_MEMORY> and returns the result.
998		1113
999	=item $device = $device->parent_device_ext	1114	=item $device = $device->parent_device_ext
1000		1115
1001	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARENT_DEVICE_EXT> and returns the result.	1116	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PARENT_DEVICE_EXT> and returns the result.
1002		1117
1003	=item @device_partition_property_exts = $device->partition_types_ext	1118	=item @device_partition_property_exts = $device->partition_types_ext
1004		1119
1005	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_TYPES_EXT> and returns the result.	1120	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PARTITION_TYPES_EXT> and returns the result.
1006		1121
1007	=item @device_partition_property_exts = $device->affinity_domains_ext	1122	=item @device_partition_property_exts = $device->affinity_domains_ext
1008		1123
1009	Calls C<clGetDeviceInfo> with C<CL_DEVICE_AFFINITY_DOMAINS_EXT> and returns the result.	1124	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_AFFINITY_DOMAINS_EXT> and returns the result.
1010		1125
1011	=item $uint = $device->reference_count_ext	1126	=item $uint = $device->reference_count_ext
1012		1127
1013	Calls C<clGetDeviceInfo> with C<CL_DEVICE_REFERENCE_COUNT_EXT> and returns the result.	1128	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_REFERENCE_COUNT_EXT> and returns the result.
1014		1129
1015	=item @device_partition_property_exts = $device->partition_style_ext	1130	=item @device_partition_property_exts = $device->partition_style_ext
1016		1131
1017	Calls C<clGetDeviceInfo> with C<CL_DEVICE_PARTITION_STYLE_EXT> and returns the result.	1132	Calls C<clGetDeviceInfo> with C<OpenCL::DEVICE_PARTITION_STYLE_EXT> and returns the result.
1018		1133
1019	=for gengetinfo end device	1134	=for gengetinfo end device
1020		1135
1021	=back	1136	=back
1022		1137
1023	=head2 THE OpenCL::Context CLASS	1138	=head2 THE OpenCL::Context CLASS
		1139
		1140	An OpenCL::Context is basically a container, or manager, for a number of
		1141	devices of a platform. It is used to create all sorts of secondary objects
		1142	such as buffers, queues, programs and so on.
		1143
		1144	All context creation functions and methods take a list of properties
		1145	(type-value pairs). All property values can be specified as integers -
		1146	some additionally support other types:
		1147
		1148	=over 4
		1149
		1150	=item OpenCL::CONTEXT_PLATFORM
		1151
		1152	Also accepts OpenCL::Platform objects.
		1153
		1154	=item OpenCL::GLX_DISPLAY_KHR
		1155
		1156	Also accepts C<undef>, in which case a deep and troubling hack is engaged
		1157	to find the current glx display (see L<GLX SUPPORT>).
		1158
		1159	=item OpenCL::GL_CONTEXT_KHR
		1160
		1161	Also accepts C<undef>, in which case a deep and troubling hack is engaged
		1162	to find the current glx context (see L<GLX SUPPORT>).
		1163
		1164	=back
1024		1165
1025	=over 4	1166	=over 4
1026		1167
1027	=item $prog = $ctx->build_program ($program, $options = "")	1168	=item $prog = $ctx->build_program ($program, $options = "")
1028		1169
…		…
1076	=item $buf = $ctx->buffer ($flags, $len)	1217	=item $buf = $ctx->buffer ($flags, $len)
1077		1218
1078	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object with the	1219	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object with the
1079	given flags and octet-size.	1220	given flags and octet-size.
1080		1221
		1222	flags: OpenCL::MEM_READ_WRITE, OpenCL::MEM_WRITE_ONLY, OpenCL::MEM_READ_ONLY,
		1223	OpenCL::MEM_USE_HOST_PTR, OpenCL::MEM_ALLOC_HOST_PTR, OpenCL::MEM_COPY_HOST_PTR,
		1224	OpenCL::MEM_HOST_WRITE_ONLY, OpenCL::MEM_HOST_READ_ONLY, OpenCL::MEM_HOST_NO_ACCESS.
		1225
1081	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateBuffer.html>	1226	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateBuffer.html>
		1227
		1228	A somewhat informative thread on the flags is:
		1229
		1230	L<http://www.khronos.org/message_boards/viewtopic.php?f=28&t=2440>
1082		1231
1083	=item $buf = $ctx->buffer_sv ($flags, $data)	1232	=item $buf = $ctx->buffer_sv ($flags, $data)
1084		1233
1085	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object and	1234	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object and
1086	initialise it with the given data values.	1235	initialise it with the given data values.
…		…
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)	1237	=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		1238
1090	Creates a new OpenCL::Image object and optionally initialises it with	1239	Creates a new OpenCL::Image object and optionally initialises it with
1091	the given data values.	1240	the given data values.
1092		1241
		1242	channel_order: OpenCL::R, OpenCL::A, OpenCL::RG, OpenCL::RA, OpenCL::RGB,
		1243	OpenCL::RGBA, OpenCL::BGRA, OpenCL::ARGB, OpenCL::INTENSITY, OpenCL::LUMINANCE,
		1244	OpenCL::Rx, OpenCL::RGx, OpenCL::RGBx.
		1245
		1246	channel_type: OpenCL::SNORM_INT8, OpenCL::SNORM_INT16, OpenCL::UNORM_INT8,
		1247	OpenCL::UNORM_INT16, OpenCL::UNORM_SHORT_565, OpenCL::UNORM_SHORT_555,
		1248	OpenCL::UNORM_INT_101010, OpenCL::SIGNED_INT8, OpenCL::SIGNED_INT16,
		1249	OpenCL::SIGNED_INT32, OpenCL::UNSIGNED_INT8, OpenCL::UNSIGNED_INT16,
		1250	OpenCL::UNSIGNED_INT32, OpenCL::HALF_FLOAT, OpenCL::FLOAT.
		1251
		1252	type: OpenCL::MEM_OBJECT_BUFFER, OpenCL::MEM_OBJECT_IMAGE2D,
		1253	OpenCL::MEM_OBJECT_IMAGE3D, OpenCL::MEM_OBJECT_IMAGE2D_ARRAY,
		1254	OpenCL::MEM_OBJECT_IMAGE1D, OpenCL::MEM_OBJECT_IMAGE1D_ARRAY,
		1255	OpenCL::MEM_OBJECT_IMAGE1D_BUFFER.
		1256
1093	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateImage.html>	1257	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateImage.html>
1094		1258
1095	=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef)	1259	=item $img = $ctx->image2d ($flags, $channel_order, $channel_type, $width, $height, $row_pitch = 0, $data = undef)
1096		1260
1097	Creates a new OpenCL::Image2D object and optionally initialises it with	1261	Creates a new OpenCL::Image2D object and optionally initialises it with
…		…
1109	=item $buffer = $ctx->gl_buffer ($flags, $bufobj)	1273	=item $buffer = $ctx->gl_buffer ($flags, $bufobj)
1110		1274
1111	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object that refers to the given	1275	Creates a new OpenCL::Buffer (actually OpenCL::BufferObj) object that refers to the given
1112	OpenGL buffer object.	1276	OpenGL buffer object.
1113		1277
		1278	flags: OpenCL::MEM_READ_WRITE, OpenCL::MEM_READ_ONLY, OpenCL::MEM_WRITE_ONLY.
		1279
1114	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLBuffer.html	1280	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateFromGLBuffer.html
1115		1281
1116	=item $img = $ctx->gl_texture ($flags, $target, $miplevel, $texture)	1282	=item $img = $ctx->gl_texture ($flags, $target, $miplevel, $texture)
1117		1283
1118	Creates a new OpenCL::Image object that refers to the given OpenGL	1284	Creates a new OpenCL::Image object that refers to the given OpenGL
1119	texture object or buffer.	1285	texture object or buffer.
1120		1286
		1287	target: GL_TEXTURE_1D, GL_TEXTURE_1D_ARRAY, GL_TEXTURE_BUFFER,
		1288	GL_TEXTURE_2D, GL_TEXTURE_2D_ARRAY, GL_TEXTURE_3D,
		1289	GL_TEXTURE_CUBE_MAP_POSITIVE_X, GL_TEXTURE_CUBE_MAP_POSITIVE_Y,
		1290	GL_TEXTURE_CUBE_MAP_POSITIVE_Z, GL_TEXTURE_CUBE_MAP_NEGATIVE_X,
		1291	GL_TEXTURE_CUBE_MAP_NEGATIVE_Y, GL_TEXTURE_CUBE_MAP_NEGATIVE_Z,
		1292	GL_TEXTURE_RECTANGLE/GL_TEXTURE_RECTANGLE_ARB.
		1293
1121	http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateFromGLTexture.html	1294	http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateFromGLTexture.html
1122		1295
1123	=item $img = $ctx->gl_texture2d ($flags, $target, $miplevel, $texture)	1296	=item $img = $ctx->gl_texture2d ($flags, $target, $miplevel, $texture)
1124		1297
1125	Creates a new OpenCL::Image2D object that refers to the given OpenGL	1298	Creates a new OpenCL::Image2D object that refers to the given OpenGL
…		…
1150		1323
1151	=item $sampler = $ctx->sampler ($normalized_coords, $addressing_mode, $filter_mode)	1324	=item $sampler = $ctx->sampler ($normalized_coords, $addressing_mode, $filter_mode)
1152		1325
1153	Creates a new OpenCL::Sampler object.	1326	Creates a new OpenCL::Sampler object.
1154		1327
		1328	addressing_mode: OpenCL::ADDRESS_NONE, OpenCL::ADDRESS_CLAMP_TO_EDGE,
		1329	OpenCL::ADDRESS_CLAMP, OpenCL::ADDRESS_REPEAT, OpenCL::ADDRESS_MIRRORED_REPEAT.
		1330
		1331	filter_mode: OpenCL::FILTER_NEAREST, OpenCL::FILTER_LINEAR.
		1332
1155	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSampler.html>	1333	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSampler.html>
1156		1334
1157	=item $program = $ctx->program_with_source ($string)	1335	=item $program = $ctx->program_with_source ($string)
1158		1336
1159	Creates a new OpenCL::Program object from the given source code.	1337	Creates a new OpenCL::Program object from the given source code.
1160		1338
1161	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateProgramWithSource.html>	1339	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateProgramWithSource.html>
1162		1340
		1341	=item ($program, \@status) = $ctx->program_with_binary (\@devices, \@binaries)
		1342
		1343	Creates a new OpenCL::Program object from the given binaries.
		1344
		1345	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateProgramWithBinary.html>
		1346
		1347	Example: clone an existing program object that contains a successfully
		1348	compiled program, no matter how useless this is.
		1349
		1350	my $clone = $ctx->program_with_binary ([$prog->devices], [$prog->binaries]);
		1351
		1352	=item $program = $ctx->program_with_built_in_kernels (\@devices, $kernel_names)
		1353
		1354	Creates a new OpenCL::Program object from the given built-in kernel names.
		1355
		1356	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCreateProgramWithBuiltInKernels.html>
		1357
		1358	=item $program = $ctx->link_program (\@devices, $options, \@programs, $cb->($program) = undef)
		1359
		1360	Links all (already compiled) program objects specified in C<@programs>
		1361	together and returns a new OpenCL::Program object with the result.
		1362
		1363	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clLinkProgram.html>
		1364
1163	=item $packed_value = $ctx->info ($name)	1365	=item $packed_value = $ctx->info ($name)
1164		1366
1165	See C<< $platform->info >> for details.	1367	See C<< $platform->info >> for details.
1166		1368
1167	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetContextInfo.html>	1369	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetContextInfo.html>
1168		1370
1169	=for gengetinfo begin context	1371	=for gengetinfo begin context
1170		1372
1171	=item $uint = $context->reference_count	1373	=item $uint = $context->reference_count
1172		1374
1173	Calls C<clGetContextInfo> with C<CL_CONTEXT_REFERENCE_COUNT> and returns the result.	1375	Calls C<clGetContextInfo> with C<OpenCL::CONTEXT_REFERENCE_COUNT> and returns the result.
1174		1376
1175	=item @devices = $context->devices	1377	=item @devices = $context->devices
1176		1378
1177	Calls C<clGetContextInfo> with C<CL_CONTEXT_DEVICES> and returns the result.	1379	Calls C<clGetContextInfo> with C<OpenCL::CONTEXT_DEVICES> and returns the result.
1178		1380
1179	=item @property_ints = $context->properties	1381	=item @property_ints = $context->properties
1180		1382
1181	Calls C<clGetContextInfo> with C<CL_CONTEXT_PROPERTIES> and returns the result.	1383	Calls C<clGetContextInfo> with C<OpenCL::CONTEXT_PROPERTIES> and returns the result.
1182		1384
1183	=item $uint = $context->num_devices	1385	=item $uint = $context->num_devices
1184		1386
1185	Calls C<clGetContextInfo> with C<CL_CONTEXT_NUM_DEVICES> and returns the result.	1387	Calls C<clGetContextInfo> with C<OpenCL::CONTEXT_NUM_DEVICES> and returns the result.
1186		1388
1187	=for gengetinfo end context	1389	=for gengetinfo end context
1188		1390
1189	=back	1391	=back
1190		1392
…		…
1229		1431
1230	=item $ev = $queue->copy_buffer ($src, $dst, $src_offset, $dst_offset, $len, $wait_events...)	1432	=item $ev = $queue->copy_buffer ($src, $dst, $src_offset, $dst_offset, $len, $wait_events...)
1231		1433
1232	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBuffer.html>	1434	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueCopyBuffer.html>
1233		1435
1234	=item $ev = $queue->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...)	1436	$eue->read_buffer_rect ($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...)
1235		1437
1236	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadBufferRect.html	1438	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueReadBufferRect.html
1237		1439
1238	=item $ev = $queue->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...)	1440	=item $ev = $queue->write_buffer_rect ($buf, $blocking, $buf_y, $host_x, $host_z, $height, $buf_row_pitch, $host_row_pitch, $data, $wait_events...)
1239		1441
1240	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteBufferRect.html	1442	http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueWriteBufferRect.html
1241		1443
1242	=item $ev = $queue->copy_buffer_to_image ($src_buffer, $dst_image, $src_offset, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $wait_events...)	1444	=item $ev = $queue->copy_buffer_to_image ($src_buffer, $dst_image, $src_offset, $dst_x, $dst_y, $dst_z, $width, $height, $depth, $wait_events...)
1243		1445
…		…
1306	reference to an array of local work sizes, with the same number of	1508	reference to an array of local work sizes, with the same number of
1307	elements as \@global_work_size.	1509	elements as \@global_work_size.
1308		1510
1309	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html>	1511	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueNDRangeKernel.html>
1310		1512
		1513	=item $ev = $queue->migrate_mem_objects (\@mem_objects, $flags, $wait_events...)
		1514
		1515	Migrates a number of OpenCL::Memory objects to or from the device.
		1516
		1517	flags: OpenCL::MIGRATE_MEM_OBJECT_HOST, OpenCL::MIGRATE_MEM_OBJECT_CONTENT_UNDEFINED
		1518
		1519	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clEnqueueMigrateMemObjects.html>
		1520
1311	=item $ev = $queue->acquire_gl_objects ([object, ...], $wait_events...)	1521	=item $ev = $queue->acquire_gl_objects ([object, ...], $wait_events...)
1312		1522
1313	Enqueues a list (an array-ref of OpenCL::Memory objects) to be acquired	1523	Enqueues a list (an array-ref of OpenCL::Memory objects) to be acquired
1314	for subsequent OpenCL usage.	1524	for subsequent OpenCL usage.
1315		1525
…		…
1350		1560
1351	=for gengetinfo begin command_queue	1561	=for gengetinfo begin command_queue
1352		1562
1353	=item $ctx = $command_queue->context	1563	=item $ctx = $command_queue->context
1354		1564
1355	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_CONTEXT> and returns the result.	1565	Calls C<clGetCommandQueueInfo> with C<OpenCL::QUEUE_CONTEXT> and returns the result.
1356		1566
1357	=item $device = $command_queue->device	1567	=item $device = $command_queue->device
1358		1568
1359	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_DEVICE> and returns the result.	1569	Calls C<clGetCommandQueueInfo> with C<OpenCL::QUEUE_DEVICE> and returns the result.
1360		1570
1361	=item $uint = $command_queue->reference_count	1571	=item $uint = $command_queue->reference_count
1362		1572
1363	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_REFERENCE_COUNT> and returns the result.	1573	Calls C<clGetCommandQueueInfo> with C<OpenCL::QUEUE_REFERENCE_COUNT> and returns the result.
1364		1574
1365	=item $command_queue_properties = $command_queue->properties	1575	=item $command_queue_properties = $command_queue->properties
1366		1576
1367	Calls C<clGetCommandQueueInfo> with C<CL_QUEUE_PROPERTIES> and returns the result.	1577	Calls C<clGetCommandQueueInfo> with C<OpenCL::QUEUE_PROPERTIES> and returns the result.
1368		1578
1369	=for gengetinfo end command_queue	1579	=for gengetinfo end command_queue
1370		1580
1371	=back	1581	=back
1372		1582
…		…
1374		1584
1375	OpenCL allows you to map buffers and images to host memory (read: perl	1585	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	1586	scalars). This is done much like reading or copying a buffer, by enqueuing
1377	a map or unmap operation on the command queue.	1587	a map or unmap operation on the command queue.
1378		1588
1379	The map operations return a C<OpenCL::Mapped> object - see L<THE	1589	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	1590	OpenCL::Mapped CLASS> section for details on what to do with these
1381	objects.	1591	objects.
1382		1592
1383	The object will be unmapped automatically when the mapped object is	1593	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,	1594	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	1595	before using the buffer in a kernel), but you can also enqueue an unmap
1386	operation manually.	1596	operation manually.
1387		1597
1388	=over 4	1598	=over 4
1389		1599
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...)	1600	=item $mapped_buffer = $queue->map_buffer ($buf, $blocking=1, $map_flags=OpenCL::MAP_READ\|OpenCL::MAP_WRITE, $offset=0, $size=undef, $wait_events...)
1391		1601
1392	Maps the given buffer into host memory and returns a C<OpenCL::MappedBuffer> object.	1602	Maps the given buffer into host memory and returns an
		1603	C<OpenCL::MappedBuffer> object. If C<$size> is specified as undef, then
		1604	the map will extend to the end of the buffer.
		1605
		1606	map_flags: OpenCL::MAP_READ, OpenCL::MAP_WRITE, OpenCL::MAP_WRITE_INVALIDATE_REGION.
1393		1607
1394	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMapBuffer.html>	1608	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMapBuffer.html>
1395		1609
		1610	Example: map the buffer $buf fully and replace the first 4 bytes by "abcd", then unmap.
		1611
		1612	{
		1613	my $mapped = $queue->map_buffer ($buf, 1, OpenCL::MAP_WRITE);
		1614	substr $$mapped, 0, 4, "abcd";
		1615	} # asynchronously unmap because $mapped is destroyed
		1616
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...)	1617	=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		1618
1398	Maps the given image area into host memory and return a	1619	Maps the given image area into host memory and return an
1399	C<OpenCL::MappedImage> object. Although there are default values for most	1620	C<OpenCL::MappedImage> object.
1400	arguments, you currently have to specify all arguments, otherwise the call	1621
1401	will fail.	1622	If any of C<$width>, C<$height> and/or C<$depth> are C<undef> then they
		1623	will be replaced by the maximum possible value.
1402		1624
1403	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMapImage.html>	1625	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clEnqueueMapImage.html>
		1626
		1627	Example: map an image (with OpenCL::UNSIGNED_INT8 channel type) and set
		1628	the first channel of the leftmost column to 5, then explicitly unmap
		1629	it. You are not necessarily meant to do it this way, this example just
		1630	shows you the accessors to use :)
		1631
		1632	my $mapped = $queue->map_image ($image, 1, OpenCL::MAP_WRITE);
		1633
		1634	$mapped->write ($_ * $mapped->row_pitch, pack "C", 5)
		1635	for 0 .. $mapped->height - 1;
		1636
		1637	$mapped->unmap;.
		1638	$mapped->wait; # only needed for out of order queues normally
1404		1639
1405	=item $ev = $queue->unmap ($mapped, $wait_events...)	1640	=item $ev = $queue->unmap ($mapped, $wait_events...)
1406		1641
1407	Unmaps the data from host memory. You must not call any methods that	1642	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	1643	modify the data, or modify the data scalar directly, after calling this
…		…
1425		1660
1426	See C<< $platform->info >> for details.	1661	See C<< $platform->info >> for details.
1427		1662
1428	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetMemObjectInfo.html>	1663	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetMemObjectInfo.html>
1429		1664
		1665	=item $memory->destructor_callback ($cb->())
		1666
		1667	Sets a callback that will be invoked after the memory object is destructed.
		1668
		1669	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetMemObjectDestructorCallback.html>
		1670
1430	=for gengetinfo begin mem	1671	=for gengetinfo begin mem
1431		1672
1432	=item $mem_object_type = $mem->type	1673	=item $mem_object_type = $mem->type
1433		1674
1434	Calls C<clGetMemObjectInfo> with C<CL_MEM_TYPE> and returns the result.	1675	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_TYPE> and returns the result.
1435		1676
1436	=item $mem_flags = $mem->flags	1677	=item $mem_flags = $mem->flags
1437		1678
1438	Calls C<clGetMemObjectInfo> with C<CL_MEM_FLAGS> and returns the result.	1679	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_FLAGS> and returns the result.
1439		1680
1440	=item $int = $mem->size	1681	=item $int = $mem->size
1441		1682
1442	Calls C<clGetMemObjectInfo> with C<CL_MEM_SIZE> and returns the result.	1683	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_SIZE> and returns the result.
1443		1684
1444	=item $ptr_value = $mem->host_ptr	1685	=item $ptr_value = $mem->host_ptr
1445		1686
1446	Calls C<clGetMemObjectInfo> with C<CL_MEM_HOST_PTR> and returns the result.	1687	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_HOST_PTR> and returns the result.
1447		1688
1448	=item $uint = $mem->map_count	1689	=item $uint = $mem->map_count
1449		1690
1450	Calls C<clGetMemObjectInfo> with C<CL_MEM_MAP_COUNT> and returns the result.	1691	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_MAP_COUNT> and returns the result.
1451		1692
1452	=item $uint = $mem->reference_count	1693	=item $uint = $mem->reference_count
1453		1694
1454	Calls C<clGetMemObjectInfo> with C<CL_MEM_REFERENCE_COUNT> and returns the result.	1695	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_REFERENCE_COUNT> and returns the result.
1455		1696
1456	=item $ctx = $mem->context	1697	=item $ctx = $mem->context
1457		1698
1458	Calls C<clGetMemObjectInfo> with C<CL_MEM_CONTEXT> and returns the result.	1699	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_CONTEXT> and returns the result.
1459		1700
1460	=item $mem = $mem->associated_memobject	1701	=item $mem = $mem->associated_memobject
1461		1702
1462	Calls C<clGetMemObjectInfo> with C<CL_MEM_ASSOCIATED_MEMOBJECT> and returns the result.	1703	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_ASSOCIATED_MEMOBJECT> and returns the result.
1463		1704
1464	=item $int = $mem->offset	1705	=item $int = $mem->offset
1465		1706
1466	Calls C<clGetMemObjectInfo> with C<CL_MEM_OFFSET> and returns the result.	1707	Calls C<clGetMemObjectInfo> with C<OpenCL::MEM_OFFSET> and returns the result.
1467		1708
1468	=for gengetinfo end mem	1709	=for gengetinfo end mem
1469		1710
1470	=item ($type, $name) = $mem->gl_object_info	1711	=item ($type, $name) = $mem->gl_object_info
1471		1712
…		…
1491	=over 4	1732	=over 4
1492		1733
1493	=item $subbuf = $buf_obj->sub_buffer_region ($flags, $origin, $size)	1734	=item $subbuf = $buf_obj->sub_buffer_region ($flags, $origin, $size)
1494		1735
1495	Creates an OpenCL::Buffer objects from this buffer and returns it. The	1736	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>.	1737	C<buffer_create_type> is assumed to be C<OpenCL::BUFFER_CREATE_TYPE_REGION>.
1497		1738
1498	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSubBuffer.html>	1739	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clCreateSubBuffer.html>
1499		1740
1500	=back	1741	=back
1501		1742
…		…
1517	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetImageInfo.html>	1758	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetImageInfo.html>
1518		1759
1519	=item ($channel_order, $channel_data_type) = $image->format	1760	=item ($channel_order, $channel_data_type) = $image->format
1520		1761
1521	Returns the channel order and type used to create the image by calling	1762	Returns the channel order and type used to create the image by calling
1522	C<clGetImageInfo> with C<CL_IMAGE_FORMAT>.	1763	C<clGetImageInfo> with C<OpenCL::IMAGE_FORMAT>.
1523		1764
1524	=for gengetinfo begin image	1765	=for gengetinfo begin image
1525		1766
1526	=item $int = $image->element_size	1767	=item $int = $image->element_size
1527		1768
1528	Calls C<clGetImageInfo> with C<CL_IMAGE_ELEMENT_SIZE> and returns the result.	1769	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_ELEMENT_SIZE> and returns the result.
1529		1770
1530	=item $int = $image->row_pitch	1771	=item $int = $image->row_pitch
1531		1772
1532	Calls C<clGetImageInfo> with C<CL_IMAGE_ROW_PITCH> and returns the result.	1773	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_ROW_PITCH> and returns the result.
1533		1774
1534	=item $int = $image->slice_pitch	1775	=item $int = $image->slice_pitch
1535		1776
1536	Calls C<clGetImageInfo> with C<CL_IMAGE_SLICE_PITCH> and returns the result.	1777	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_SLICE_PITCH> and returns the result.
1537		1778
1538	=item $int = $image->width	1779	=item $int = $image->width
1539		1780
1540	Calls C<clGetImageInfo> with C<CL_IMAGE_WIDTH> and returns the result.	1781	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_WIDTH> and returns the result.
1541		1782
1542	=item $int = $image->height	1783	=item $int = $image->height
1543		1784
1544	Calls C<clGetImageInfo> with C<CL_IMAGE_HEIGHT> and returns the result.	1785	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_HEIGHT> and returns the result.
1545		1786
1546	=item $int = $image->depth	1787	=item $int = $image->depth
1547		1788
1548	Calls C<clGetImageInfo> with C<CL_IMAGE_DEPTH> and returns the result.	1789	Calls C<clGetImageInfo> with C<OpenCL::IMAGE_DEPTH> and returns the result.
1549		1790
1550	=for gengetinfo end image	1791	=for gengetinfo end image
1551		1792
1552	=for gengetinfo begin gl_texture	1793	=for gengetinfo begin gl_texture
1553		1794
1554	=item $GLenum = $gl_texture->target	1795	=item $GLenum = $gl_texture->target
1555		1796
1556	Calls C<clGetGLTextureInfo> with C<CL_GL_TEXTURE_TARGET> and returns the result.	1797	Calls C<clGetGLTextureInfo> with C<OpenCL::GL_TEXTURE_TARGET> and returns the result.
1557		1798
1558	=item $GLint = $gl_texture->gl_mipmap_level	1799	=item $GLint = $gl_texture->gl_mipmap_level
1559		1800
1560	Calls C<clGetGLTextureInfo> with C<CL_GL_MIPMAP_LEVEL> and returns the result.	1801	Calls C<clGetGLTextureInfo> with C<OpenCL::GL_MIPMAP_LEVEL> and returns the result.
1561		1802
1562	=for gengetinfo end gl_texture	1803	=for gengetinfo end gl_texture
1563		1804
1564	=back	1805	=back
1565		1806
…		…
1575		1816
1576	=for gengetinfo begin sampler	1817	=for gengetinfo begin sampler
1577		1818
1578	=item $uint = $sampler->reference_count	1819	=item $uint = $sampler->reference_count
1579		1820
1580	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_REFERENCE_COUNT> and returns the result.	1821	Calls C<clGetSamplerInfo> with C<OpenCL::SAMPLER_REFERENCE_COUNT> and returns the result.
1581		1822
1582	=item $ctx = $sampler->context	1823	=item $ctx = $sampler->context
1583		1824
1584	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_CONTEXT> and returns the result.	1825	Calls C<clGetSamplerInfo> with C<OpenCL::SAMPLER_CONTEXT> and returns the result.
1585		1826
1586	=item $addressing_mode = $sampler->normalized_coords	1827	=item $addressing_mode = $sampler->normalized_coords
1587		1828
1588	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_NORMALIZED_COORDS> and returns the result.	1829	Calls C<clGetSamplerInfo> with C<OpenCL::SAMPLER_NORMALIZED_COORDS> and returns the result.
1589		1830
1590	=item $filter_mode = $sampler->addressing_mode	1831	=item $filter_mode = $sampler->addressing_mode
1591		1832
1592	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_ADDRESSING_MODE> and returns the result.	1833	Calls C<clGetSamplerInfo> with C<OpenCL::SAMPLER_ADDRESSING_MODE> and returns the result.
1593		1834
1594	=item $boolean = $sampler->filter_mode	1835	=item $boolean = $sampler->filter_mode
1595		1836
1596	Calls C<clGetSamplerInfo> with C<CL_SAMPLER_FILTER_MODE> and returns the result.	1837	Calls C<clGetSamplerInfo> with C<OpenCL::SAMPLER_FILTER_MODE> and returns the result.
1597		1838
1598	=for gengetinfo end sampler	1839	=for gengetinfo end sampler
1599		1840
1600	=back	1841	=back
1601		1842
…		…
1619	not so. So best make sure you don't pass in invalid values.	1860	not so. So best make sure you don't pass in invalid values.
1620		1861
1621	Some implementations fail with C<OpenCL::INVALID_BINARY> when the	1862	Some implementations fail with C<OpenCL::INVALID_BINARY> when the
1622	compilation state is successful but some later stage fails.	1863	compilation state is successful but some later stage fails.
1623		1864
		1865	options: C<-D name>, C<-D name=definition>, C<-I dir>,
		1866	C<-cl-single-precision-constant>, C<-cl-denorms-are-zero>,
		1867	C<-cl-fp32-correctly-rounded-divide-sqrt>, C<-cl-opt-disable>,
		1868	C<-cl-mad-enable>, C<-cl-no-signed-zeros>, C<-cl-unsafe-math-optimizations>,
		1869	C<-cl-finite-math-only>, C<-cl-fast-relaxed-math>,
		1870	C<-w>, C<-Werror>, C<-cl-std=CL1.1/CL1.2>, C<-cl-kernel-arg-info>,
		1871	C<-create-library>, C<-enable-link-options>.
		1872
		1873	build_status: OpenCL::BUILD_SUCCESS, OpenCL::BUILD_NONE,
		1874	OpenCL::BUILD_ERROR, OpenCL::BUILD_IN_PROGRESS.
		1875
1624	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clBuildProgram.html>	1876	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clBuildProgram.html>
1625		1877
1626	=item $program->build_async (\@devices = undef, $options = "", $cb->($program) = undef)	1878	=item $program->build_async (\@devices = undef, $options = "", $cb->($program) = undef)
1627		1879
1628	Similar to C<< ->build >>, except it starts a thread, and never fails (you	1880	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).	1881	need to check the compilation status form the callback, or by polling).
1630		1882
		1883	=item $program->compile (\@devices = undef, $options = "", \%headers = undef, $cb->($program) = undef)
		1884
		1885	Compiles the given program for the given devices (or all devices if
		1886	undef). If C<$headers> is given, it must be a hashref with include name =>
		1887	OpenCL::Program pairs.
		1888
		1889	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clCompileProgram.html>
		1890
1631	=item $packed_value = $program->build_info ($device, $name)	1891	=item $packed_value = $program->build_info ($device, $name)
1632		1892
1633	Similar to C<< $platform->info >>, but returns build info for a previous	1893	Similar to C<< $platform->info >>, but returns build info for a previous
1634	build attempt for the given device.	1894	build attempt for the given device.
1635		1895
		1896	binary_type: OpenCL::PROGRAM_BINARY_TYPE_NONE,
		1897	OpenCL::PROGRAM_BINARY_TYPE_COMPILED_OBJECT,
		1898	OpenCL::PROGRAM_BINARY_TYPE_LIBRARY,
		1899	OpenCL::PROGRAM_BINARY_TYPE_EXECUTABLE.
		1900
1636	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetBuildInfo.html>	1901	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetBuildInfo.html>
1637		1902
1638	=item $kernel = $program->kernel ($function_name)	1903	=item $kernel = $program->kernel ($function_name)
1639		1904
1640	Creates an OpenCL::Kernel object out of the named C<__kernel> function in	1905	Creates an OpenCL::Kernel object out of the named C<__kernel> function in
…		…
1650		1915
1651	=for gengetinfo begin program_build	1916	=for gengetinfo begin program_build
1652		1917
1653	=item $build_status = $program->build_status ($device)	1918	=item $build_status = $program->build_status ($device)
1654		1919
1655	Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_STATUS> and returns the result.	1920	Calls C<clGetProgramBuildInfo> with C<OpenCL::PROGRAM_BUILD_STATUS> and returns the result.
1656		1921
1657	=item $string = $program->build_options ($device)	1922	=item $string = $program->build_options ($device)
1658		1923
1659	Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_OPTIONS> and returns the result.	1924	Calls C<clGetProgramBuildInfo> with C<OpenCL::PROGRAM_BUILD_OPTIONS> and returns the result.
1660		1925
1661	=item $string = $program->build_log ($device)	1926	=item $string = $program->build_log ($device)
1662		1927
1663	Calls C<clGetProgramBuildInfo> with C<CL_PROGRAM_BUILD_LOG> and returns the result.	1928	Calls C<clGetProgramBuildInfo> with C<OpenCL::PROGRAM_BUILD_LOG> and returns the result.
		1929
		1930	=item $binary_type = $program->binary_type ($device)
		1931
		1932	Calls C<clGetProgramBuildInfo> with C<OpenCL::PROGRAM_BINARY_TYPE> and returns the result.
1664		1933
1665	=for gengetinfo end program_build	1934	=for gengetinfo end program_build
1666		1935
1667	=item $packed_value = $program->info ($name)	1936	=item $packed_value = $program->info ($name)
1668		1937
…		…
1672		1941
1673	=for gengetinfo begin program	1942	=for gengetinfo begin program
1674		1943
1675	=item $uint = $program->reference_count	1944	=item $uint = $program->reference_count
1676		1945
1677	Calls C<clGetProgramInfo> with C<CL_PROGRAM_REFERENCE_COUNT> and returns the result.	1946	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_REFERENCE_COUNT> and returns the result.
1678		1947
1679	=item $ctx = $program->context	1948	=item $ctx = $program->context
1680		1949
1681	Calls C<clGetProgramInfo> with C<CL_PROGRAM_CONTEXT> and returns the result.	1950	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_CONTEXT> and returns the result.
1682		1951
1683	=item $uint = $program->num_devices	1952	=item $uint = $program->num_devices
1684		1953
1685	Calls C<clGetProgramInfo> with C<CL_PROGRAM_NUM_DEVICES> and returns the result.	1954	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_NUM_DEVICES> and returns the result.
1686		1955
1687	=item @devices = $program->devices	1956	=item @devices = $program->devices
1688		1957
1689	Calls C<clGetProgramInfo> with C<CL_PROGRAM_DEVICES> and returns the result.	1958	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_DEVICES> and returns the result.
1690		1959
1691	=item $string = $program->source	1960	=item $string = $program->source
1692		1961
1693	Calls C<clGetProgramInfo> with C<CL_PROGRAM_SOURCE> and returns the result.	1962	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_SOURCE> and returns the result.
1694		1963
1695	=item @ints = $program->binary_sizes	1964	=item @ints = $program->binary_sizes
1696		1965
1697	Calls C<clGetProgramInfo> with C<CL_PROGRAM_BINARY_SIZES> and returns the result.	1966	Calls C<clGetProgramInfo> with C<OpenCL::PROGRAM_BINARY_SIZES> and returns the result.
1698		1967
1699	=for gengetinfo end program	1968	=for gengetinfo end program
1700		1969
1701	=item @blobs = $program->binaries	1970	=item @blobs = $program->binaries
1702		1971
…		…
1723		1992
1724	=for gengetinfo begin kernel	1993	=for gengetinfo begin kernel
1725		1994
1726	=item $string = $kernel->function_name	1995	=item $string = $kernel->function_name
1727		1996
1728	Calls C<clGetKernelInfo> with C<CL_KERNEL_FUNCTION_NAME> and returns the result.	1997	Calls C<clGetKernelInfo> with C<OpenCL::KERNEL_FUNCTION_NAME> and returns the result.
1729		1998
1730	=item $uint = $kernel->num_args	1999	=item $uint = $kernel->num_args
1731		2000
1732	Calls C<clGetKernelInfo> with C<CL_KERNEL_NUM_ARGS> and returns the result.	2001	Calls C<clGetKernelInfo> with C<OpenCL::KERNEL_NUM_ARGS> and returns the result.
1733		2002
1734	=item $uint = $kernel->reference_count	2003	=item $uint = $kernel->reference_count
1735		2004
1736	Calls C<clGetKernelInfo> with C<CL_KERNEL_REFERENCE_COUNT> and returns the result.	2005	Calls C<clGetKernelInfo> with C<OpenCL::KERNEL_REFERENCE_COUNT> and returns the result.
1737		2006
1738	=item $ctx = $kernel->context	2007	=item $ctx = $kernel->context
1739		2008
1740	Calls C<clGetKernelInfo> with C<CL_KERNEL_CONTEXT> and returns the result.	2009	Calls C<clGetKernelInfo> with C<OpenCL::KERNEL_CONTEXT> and returns the result.
1741		2010
1742	=item $program = $kernel->program	2011	=item $program = $kernel->program
1743		2012
1744	Calls C<clGetKernelInfo> with C<CL_KERNEL_PROGRAM> and returns the result.	2013	Calls C<clGetKernelInfo> with C<OpenCL::KERNEL_PROGRAM> and returns the result.
1745		2014
1746	=for gengetinfo end kernel	2015	=for gengetinfo end kernel
1747		2016
1748	=item $packed_value = $kernel->work_group_info ($device, $name)	2017	=item $packed_value = $kernel->work_group_info ($device, $name)
1749		2018
1750	See C<< $platform->info >> for details.	2019	See C<< $platform->info >> for details.
1751		2020
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>	2021	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clGetKernelWorkGroupInfo.html>
1756		2022
1757	=for gengetinfo begin kernel_work_group	2023	=for gengetinfo begin kernel_work_group
1758		2024
1759	=item $int = $kernel->work_group_size ($device)	2025	=item $int = $kernel->work_group_size ($device)
1760		2026
1761	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_WORK_GROUP_SIZE> and returns the result.	2027	Calls C<clGetKernelWorkGroupInfo> with C<OpenCL::KERNEL_WORK_GROUP_SIZE> and returns the result.
1762		2028
1763	=item @ints = $kernel->compile_work_group_size ($device)	2029	=item @ints = $kernel->compile_work_group_size ($device)
1764		2030
1765	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_COMPILE_WORK_GROUP_SIZE> and returns the result.	2031	Calls C<clGetKernelWorkGroupInfo> with C<OpenCL::KERNEL_COMPILE_WORK_GROUP_SIZE> and returns the result.
1766		2032
1767	=item $ulong = $kernel->local_mem_size ($device)	2033	=item $ulong = $kernel->local_mem_size ($device)
1768		2034
1769	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_LOCAL_MEM_SIZE> and returns the result.	2035	Calls C<clGetKernelWorkGroupInfo> with C<OpenCL::KERNEL_LOCAL_MEM_SIZE> and returns the result.
1770		2036
1771	=item $int = $kernel->preferred_work_group_size_multiple ($device)	2037	=item $int = $kernel->preferred_work_group_size_multiple ($device)
1772		2038
1773	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE> and returns the result.	2039	Calls C<clGetKernelWorkGroupInfo> with C<OpenCL::KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE> and returns the result.
1774		2040
1775	=item $ulong = $kernel->private_mem_size ($device)	2041	=item $ulong = $kernel->private_mem_size ($device)
1776		2042
1777	Calls C<clGetKernelWorkGroupInfo> with C<CL_KERNEL_PRIVATE_MEM_SIZE> and returns the result.	2043	Calls C<clGetKernelWorkGroupInfo> with C<OpenCL::KERNEL_PRIVATE_MEM_SIZE> and returns the result.
1778		2044
1779	=for gengetinfo end kernel_work_group	2045	=for gengetinfo end kernel_work_group
		2046
		2047	=item $packed_value = $kernel->arg_info ($idx, $name)
		2048
		2049	See C<< $platform->info >> for details.
		2050
		2051	L<http://www.khronos.org/registry/cl/sdk/1.2/docs/man/xhtml/clGetKernelArgInfo.html>
		2052
		2053	=for gengetinfo begin kernel_arg
		2054
		2055	=item $kernel_arg_address_qualifier = $kernel->arg_address_qualifier ($idx)
		2056
		2057	Calls C<clGetKernelArgInfo> with C<OpenCL::KERNEL_ARG_ADDRESS_QUALIFIER> and returns the result.
		2058
		2059	=item $kernel_arg_access_qualifier = $kernel->arg_access_qualifier ($idx)
		2060
		2061	Calls C<clGetKernelArgInfo> with C<OpenCL::KERNEL_ARG_ACCESS_QUALIFIER> and returns the result.
		2062
		2063	=item $string = $kernel->arg_type_name ($idx)
		2064
		2065	Calls C<clGetKernelArgInfo> with C<OpenCL::KERNEL_ARG_TYPE_NAME> and returns the result.
		2066
		2067	=item $kernel_arg_type_qualifier = $kernel->arg_type_qualifier ($idx)
		2068
		2069	Calls C<clGetKernelArgInfo> with C<OpenCL::KERNEL_ARG_TYPE_QUALIFIER> and returns the result.
		2070
		2071	=item $string = $kernel->arg_name ($idx)
		2072
		2073	Calls C<clGetKernelArgInfo> with C<OpenCL::KERNEL_ARG_NAME> and returns the result.
		2074
		2075	=for gengetinfo end kernel_arg
1780		2076
1781	=item $kernel->setf ($format, ...)	2077	=item $kernel->setf ($format, ...)
1782		2078
1783	Sets the arguments of a kernel. Since OpenCL 1.1 doesn't have a generic	2079	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	2080	way to set arguments (and with OpenCL 1.2 it might be rather slow), you
…		…
1896		2192
1897	=for gengetinfo begin event	2193	=for gengetinfo begin event
1898		2194
1899	=item $queue = $event->command_queue	2195	=item $queue = $event->command_queue
1900		2196
1901	Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_QUEUE> and returns the result.	2197	Calls C<clGetEventInfo> with C<OpenCL::EVENT_COMMAND_QUEUE> and returns the result.
1902		2198
1903	=item $command_type = $event->command_type	2199	=item $command_type = $event->command_type
1904		2200
1905	Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_TYPE> and returns the result.	2201	Calls C<clGetEventInfo> with C<OpenCL::EVENT_COMMAND_TYPE> and returns the result.
1906		2202
1907	=item $uint = $event->reference_count	2203	=item $uint = $event->reference_count
1908		2204
1909	Calls C<clGetEventInfo> with C<CL_EVENT_REFERENCE_COUNT> and returns the result.	2205	Calls C<clGetEventInfo> with C<OpenCL::EVENT_REFERENCE_COUNT> and returns the result.
1910		2206
1911	=item $uint = $event->command_execution_status	2207	=item $uint = $event->command_execution_status
1912		2208
1913	Calls C<clGetEventInfo> with C<CL_EVENT_COMMAND_EXECUTION_STATUS> and returns the result.	2209	Calls C<clGetEventInfo> with C<OpenCL::EVENT_COMMAND_EXECUTION_STATUS> and returns the result.
1914		2210
1915	=item $ctx = $event->context	2211	=item $ctx = $event->context
1916		2212
1917	Calls C<clGetEventInfo> with C<CL_EVENT_CONTEXT> and returns the result.	2213	Calls C<clGetEventInfo> with C<OpenCL::EVENT_CONTEXT> and returns the result.
1918		2214
1919	=for gengetinfo end event	2215	=for gengetinfo end event
1920		2216
1921	=item $packed_value = $ev->profiling_info ($name)	2217	=item $packed_value = $ev->profiling_info ($name)
1922		2218
…		…
1929		2225
1930	=for gengetinfo begin profiling	2226	=for gengetinfo begin profiling
1931		2227
1932	=item $ulong = $event->profiling_command_queued	2228	=item $ulong = $event->profiling_command_queued
1933		2229
1934	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_QUEUED> and returns the result.	2230	Calls C<clGetEventProfilingInfo> with C<OpenCL::PROFILING_COMMAND_QUEUED> and returns the result.
1935		2231
1936	=item $ulong = $event->profiling_command_submit	2232	=item $ulong = $event->profiling_command_submit
1937		2233
1938	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_SUBMIT> and returns the result.	2234	Calls C<clGetEventProfilingInfo> with C<OpenCL::PROFILING_COMMAND_SUBMIT> and returns the result.
1939		2235
1940	=item $ulong = $event->profiling_command_start	2236	=item $ulong = $event->profiling_command_start
1941		2237
1942	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_START> and returns the result.	2238	Calls C<clGetEventProfilingInfo> with C<OpenCL::PROFILING_COMMAND_START> and returns the result.
1943		2239
1944	=item $ulong = $event->profiling_command_end	2240	=item $ulong = $event->profiling_command_end
1945		2241
1946	Calls C<clGetEventProfilingInfo> with C<CL_PROFILING_COMMAND_END> and returns the result.	2242	Calls C<clGetEventProfilingInfo> with C<OpenCL::PROFILING_COMMAND_END> and returns the result.
1947		2243
1948	=for gengetinfo end profiling	2244	=for gengetinfo end profiling
1949		2245
1950	=back	2246	=back
1951		2247
…		…
1957		2253
1958	=item $ev->set_status ($execution_status)	2254	=item $ev->set_status ($execution_status)
1959		2255
1960	Sets the execution status of the user event. Can only be called once,	2256	Sets the execution status of the user event. Can only be called once,
1961	either with OpenCL::COMPLETE or a negative number as status.	2257	either with OpenCL::COMPLETE or a negative number as status.
		2258
		2259	execution_status: OpenCL::COMPLETE or a negative integer.
1962		2260
1963	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetUserEventStatus.html>	2261	L<http://www.khronos.org/registry/cl/sdk/1.1/docs/man/xhtml/clSetUserEventStatus.html>
1964		2262
1965	=back	2263	=back
1966		2264
…		…
2020		2318
2021	Returns the size of the mapped area, in bytes. Same as C<length $$mapped>.	2319	Returns the size of the mapped area, in bytes. Same as C<length $$mapped>.
2022		2320
2023	=item $ptr = $mapped->ptr	2321	=item $ptr = $mapped->ptr
2024		2322
2025	Returns the raw memory address of the mapped area - same as C<$mapped+0>.	2323	Returns the raw memory address of the mapped area.
2026		2324
2027	=item $mapped->set ($offset, $data)	2325	=item $mapped->set ($offset, $data)
2028		2326
2029	Replaces the data at the given C<$offset> in the memory area by the new	2327	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	2328	C<$data>. This method is safer than direct manipulation of C<$mapped>
2031	C<$$mapped> with substr.	2329	because it does bounds-checking, but also slower.
2032		2330
2033	=item $data = $mapped->get ($offset, $length)	2331	=item $data = $mapped->get ($offset, $length)
2034		2332
2035	Returns (without copying) a scalar representing the data at the given	2333	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	2334	C<$offset> and C<$length> in the mapped memory area. This is the same as
2037	the following substr, except much slower:	2335	the following substr, except much slower;
2038		2336
2039	$data = substr $$mapped, $offset, $length	2337	$data = substr $$mapped, $offset, $length
2040		2338
2041	#TODO: really?
2042
2043	=cut	2339	=cut
2044		2340
2045	sub get {	2341	sub OpenCL::Mapped::get {
2046	substr ${$_[0]}, $_[1], $_[2]	2342	substr ${$_[0]}, $_[1], $_[2]
2047	}	2343	}
2048		2344
2049	=back	2345	=back
2050		2346
…		…
2056		2352
2057	This is a subclass of OpenCL::Mapped, representing mapped images.	2353	This is a subclass of OpenCL::Mapped, representing mapped images.
2058		2354
2059	=over 4	2355	=over 4
2060		2356
		2357	=item $pixels = $mapped->width
		2358
		2359	=item $pixels = $mapped->height
		2360
		2361	=item $pixels = $mapped->depth
		2362
		2363	Return the width/height/depth of the mapped image region, in pixels.
		2364
2061	=item $bytes = $mapped->row_pitch	2365	=item $bytes = $mapped->row_pitch
2062		2366
2063	=item $bytes = $mapped->slice_pitch	2367	=item $bytes = $mapped->slice_pitch
2064		2368
2065	Return the row or slice pitch of the image that has been mapped.	2369	Return the row or slice pitch of the image that has been mapped.
2066		2370
		2371	=item $bytes = $mapped->element_size
		2372
		2373	Return the size of a single pixel.
		2374
		2375	=item $data = $mapped->get_row ($count, $x=0, $y=0, $z=0)
		2376
		2377	Return C<$count> pixels from the given coordinates. The pixel data must
		2378	be completely contained within a single row.
		2379
		2380	If C<$count> is C<undef>, then all the remaining pixels in that row are
		2381	returned.
		2382
		2383	=item $mapped->set_row ($data, $x=0, $y=0, $z=0)
		2384
		2385	Write the given pixel data at the given coordinate. The pixel data must
		2386	be completely contained within a single row.
		2387
2067	=back	2388	=back
2068
2069		2389
2070	=cut	2390	=cut
2071		2391
2072	1;	2392	1;
2073		2393

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.88 by root, Tue Oct 22 17:25:38 2013 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.88 by root, Tue Oct 22 17:25:38 2013 UTC