ViewVC Help

View File | Revision Log | Show Annotations | Download File

/cvs/OpenCL/OpenCL.xs

Comparing OpenCL/OpenCL.xs (file contents):
Revision 1.2 by root, Tue Nov 15 09:24:40 2011 UTC vs.
Revision 1.14 by root, Sun Nov 20 10:21:27 2011 UTC

…		…
7	typedef cl_platform_id OpenCL__Platform;	7	typedef cl_platform_id OpenCL__Platform;
8	typedef cl_device_id OpenCL__Device;	8	typedef cl_device_id OpenCL__Device;
9	typedef cl_context OpenCL__Context;	9	typedef cl_context OpenCL__Context;
10	typedef cl_command_queue OpenCL__Queue;	10	typedef cl_command_queue OpenCL__Queue;
11	typedef cl_mem OpenCL__Memory;	11	typedef cl_mem OpenCL__Memory;
		12	typedef cl_mem OpenCL__Buffer;
		13	typedef cl_mem OpenCL__Image;
		14	typedef cl_mem OpenCL__Image2D;
		15	typedef cl_mem OpenCL__Image3D;
		16	typedef cl_mem OpenCL__Memory_ornull;
		17	typedef cl_mem OpenCL__Buffer_ornull;
		18	typedef cl_mem OpenCL__Image_ornull;
		19	typedef cl_mem OpenCL__Image2D_ornull;
		20	typedef cl_mem OpenCL__Image3D_ornull;
12	typedef cl_sampler OpenCL__Sampler;	21	typedef cl_sampler OpenCL__Sampler;
13	typedef cl_program OpenCL__Program;	22	typedef cl_program OpenCL__Program;
14	typedef cl_kernel OpenCL__Kernel;	23	typedef cl_kernel OpenCL__Kernel;
15	typedef cl_event OpenCL__Event;	24	typedef cl_event OpenCL__Event;
		25	typedef cl_event OpenCL__UserEvent;
16		26
17	static const struct {	27	typedef SV *FUTURE;
		28
		29	/*****************************************************************************/
		30
		31	/* up to two temporary buffers */
		32	static void *
		33	tmpbuf (size_t size)
		34	{
		35	static int idx;
		36	static void *buf [2];
		37	static size_t len [2];
		38
		39	idx ^= 1;
		40
		41	if (len [idx] < size)
		42	{
		43	free (buf [idx]);
		44	len [idx] = ((size + 31) & ~4095) + 4096 - 32;
		45	buf [idx] = malloc (len [idx]);
		46	}
		47
		48	return buf [idx];
		49	}
		50
		51	/*****************************************************************************/
		52
		53	typedef struct
		54	{
18	IV iv;	55	IV iv;
19	const char *name;	56	const char *name;
20	} cl_error[] = {
21	#define def_error(name) { (IV)CL_ ## name, # name },	57	#define const_iv(name) { (IV)CL_ ## name, # name },
22	#include "invalid.h"	58	} ivstr;
23	};
24		59
25	static const char *	60	static const char *
26	clstrerror (cl_int res)	61	iv2str (IV value, const ivstr *base, int count, const char *fallback)
27	{	62	{
28	int i;	63	int i;
29	static char numbuf [32];	64	static char strbuf [32];
30		65
31	for (i = sizeof (cl_error) / sizeof (cl_error [0]); i--; )	66	for (i = count; i--; )
32	if (cl_error [i].iv == res)	67	if (base [i].iv == value)
33	return cl_error [i].name;	68	return base [i].name;
34		69
35	snprintf (numbuf, sizeof (numbuf), "ERROR(%d)", res);	70	snprintf (strbuf, sizeof (strbuf), fallback, (int)value);
36		71
37	return numbuf;	72	return strbuf;
38	}	73	}
39		74
		75	static const char *
		76	enum2str (cl_uint value)
		77	{
		78	static const ivstr enumstr[] = {
		79	#include "enumstr.h"
		80	};
		81
		82	return iv2str (value, enumstr, sizeof (enumstr) / sizeof (enumstr [0]), "ENUM(0x%04x)");
		83	}
		84
		85	static const char *
		86	err2str (cl_int err)
		87	{
		88	static const ivstr errstr[] = {
		89	#include "errstr.h"
		90	};
		91
		92	return iv2str (err, errstr, sizeof (errstr) / sizeof (errstr [0]), "ERROR(%d)");
		93	}
		94
		95	/*****************************************************************************/
		96
		97	static cl_int res;
		98
40	#define FAIL(name,res) \	99	#define FAIL(name) \
41	croak ("cl" # name ": %s", clstrerror (res));	100	croak ("cl" # name ": %s", err2str (res));
42		101
43	#define NEED_SUCCESS(name,args) \	102	#define NEED_SUCCESS(name,args) \
44	do { \	103	do { \
45	cl_int res = cl ## name args; \	104	res = cl ## name args; \
46	\	105	\
47	if (res) \	106	if (res) \
48	FAIL (name, res); \	107	FAIL (name); \
49	} while (0)	108	} while (0)
		109
		110	#define NEED_SUCCESS_ARG(retdecl, name, args) \
		111	retdecl = cl ## name args; \
		112	if (res) \
		113	FAIL (name);
		114
		115	/*****************************************************************************/
50		116
51	#define NEW_MORTAL_OBJ(class,ptr) sv_setref_pv (sv_newmortal (), class, ptr)	117	#define NEW_MORTAL_OBJ(class,ptr) sv_setref_pv (sv_newmortal (), class, ptr)
52	#define XPUSH_NEW_OBJ(class,ptr) XPUSHs (NEW_MORTAL_OBJ (class, ptr))	118	#define XPUSH_NEW_OBJ(class,ptr) XPUSHs (NEW_MORTAL_OBJ (class, ptr))
53		119
54	/*TODO*/	120	static void *
55	#define EVENT_LIST(items,count) cl_uint event_list_count = 0; cl_event *event_list_ptr = 0	121	SvPTROBJ (const char *func, const char *svname, SV *sv, const char *pkg)
		122	{
		123	if (SvROK (sv) && sv_derived_from (sv, pkg))
		124	return (void *)SvIV (SvRV (sv));
		125
		126	croak ("%s: %s is not of type %s", func, svname, pkg);
		127	}
		128
		129	/*****************************************************************************/
		130
		131	static size_t
		132	img_row_pitch (cl_mem img)
		133	{
		134	size_t res;
		135	clGetImageInfo (img, CL_IMAGE_ROW_PITCH, sizeof (res), &res, 0);
		136	return res;
		137	}
		138
		139	static cl_event *
		140	event_list (SV **items, int count)
		141	{
		142	cl_event *list = tmpbuf (sizeof (cl_event) * count);
		143
		144	while (count--)
		145	list [count] = SvPTROBJ ("clEnqueue", "wait_events", items [count], "OpenCL::Event");
		146
		147	return list;
		148	}
		149
		150	#define EVENT_LIST(items,count) \
		151	cl_uint event_list_count = (count); \
		152	cl_event *event_list_ptr = event_list (&ST (items), event_list_count)
56		153
57	#define INFO(class) \	154	#define INFO(class) \
58	{ \	155	{ \
59	size_t size; \	156	size_t size; \
60	SV *sv; \
61	\
62	NEED_SUCCESS (Get ## class ## Info, (this, name, 0, 0, &size)); \	157	NEED_SUCCESS (Get ## class ## Info, (this, name, 0, 0, &size)); \
63	sv = sv_2mortal (newSV (size)); \	158	SV *sv = sv_2mortal (newSV (size)); \
64	SvUPGRADE (sv, SVt_PV); \	159	SvUPGRADE (sv, SVt_PV); \
65	SvPOK_only (sv); \	160	SvPOK_only (sv); \
66	SvCUR_set (sv, size); \	161	SvCUR_set (sv, size); \
67	NEED_SUCCESS (Get ## class ## Info, (this, name, size, SvPVX (sv), 0)); \	162	NEED_SUCCESS (Get ## class ## Info, (this, name, size, SvPVX (sv), 0)); \
68	XPUSHs (sv); \	163	XPUSHs (sv); \
…		…
73	PROTOTYPES: ENABLE	168	PROTOTYPES: ENABLE
74		169
75	BOOT:	170	BOOT:
76	{	171	{
77	HV *stash = gv_stashpv ("OpenCL", 1);	172	HV *stash = gv_stashpv ("OpenCL", 1);
78	static const struct {
79	const char *name;
80	IV iv;
81	} *civ, const_iv[] = {	173	static const ivstr *civ, const_iv[] = {
82	#define const_iv(name) { # name, (IV)CL_ ## name },	174	{ sizeof (cl_char ), "SIZEOF_CHAR" },
		175	{ sizeof (cl_uchar ), "SIZEOF_UCHAR" },
		176	{ sizeof (cl_short ), "SIZEOF_SHORT" },
		177	{ sizeof (cl_ushort), "SIZEOF_USHORT" },
		178	{ sizeof (cl_int ), "SIZEOF_INT" },
		179	{ sizeof (cl_uint ), "SIZEOF_UINT" },
		180	{ sizeof (cl_long ), "SIZEOF_LONG" },
		181	{ sizeof (cl_ulong ), "SIZEOF_ULONG" },
		182	{ sizeof (cl_half ), "SIZEOF_HALF" },
		183	{ sizeof (cl_float ), "SIZEOF_FLOAT" },
		184	{ sizeof (cl_double), "SIZEOF_DOUBLE" },
83	#include "constiv.h"	185	#include "constiv.h"
84	};	186	};
85	for (civ = const_iv + sizeof (const_iv) / sizeof (const_iv [0]); civ > const_iv; civ--)	187	for (civ = const_iv + sizeof (const_iv) / sizeof (const_iv [0]); civ > const_iv; civ--)
86	newCONSTSUB (stash, (char *)civ[-1].name, newSViv (civ[-1].iv));	188	newCONSTSUB (stash, (char *)civ[-1].name, newSViv (civ[-1].iv));
87	}	189	}
88		190
		191	cl_int
		192	errno ()
		193	CODE:
		194	errno = res;
		195
		196	const char *
		197	err2str (cl_int err)
		198
		199	const char *
		200	enum2str (cl_uint value)
		201
89	void	202	void
90	platforms ()	203	platforms ()
91	PPCODE:	204	PPCODE:
92	{
93	cl_platform_id *list;	205	cl_platform_id *list;
94	cl_uint count;	206	cl_uint count;
95	int i;	207	int i;
96		208
97	NEED_SUCCESS (GetPlatformIDs, (0, 0, &count));	209	NEED_SUCCESS (GetPlatformIDs, (0, 0, &count));
98	Newx (list, count, cl_platform_id);	210	list = tmpbuf (sizeof (*list) * count);
99	NEED_SUCCESS (GetPlatformIDs, (count, list, 0));	211	NEED_SUCCESS (GetPlatformIDs, (count, list, 0));
100		212
101	EXTEND (SP, count);	213	EXTEND (SP, count);
102	for (i = 0; i < count; ++i)	214	for (i = 0; i < count; ++i)
103	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Platform", list [i]));	215	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Platform", list [i]));
104		216
105	Safefree (list);
106	}
107
108	void	217	void
109	context_from_type_simple (cl_device_type type = CL_DEVICE_TYPE_DEFAULT)	218	context_from_type (FUTURE properties = 0, cl_device_type type = CL_DEVICE_TYPE_DEFAULT, FUTURE notify = 0)
110	PPCODE:	219	PPCODE:
111	{
112	cl_int res;
113	cl_context ctx = clCreateContextFromType (0, type, 0, 0, &res);	220	NEED_SUCCESS_ARG (cl_context ctx, CreateContextFromType, (0, type, 0, 0, &res));
114
115	if (res)
116	FAIL (CreateContextFromType, res);
117
118	XPUSH_NEW_OBJ ("OpenCL::Context", ctx);	221	XPUSH_NEW_OBJ ("OpenCL::Context", ctx);
119	}	222
		223	void
		224	context (FUTURE properties, FUTURE devices, FUTURE notify = 0)
		225	PPCODE:
		226	/* der Gipfel der Kunst */
120		227
121	void	228	void
122	wait_for_events (...)	229	wait_for_events (...)
123	CODE:	230	CODE:
124	{
125	EVENT_LIST (0, items);	231	EVENT_LIST (0, items);
126	NEED_SUCCESS (WaitForEvents, (event_list_count, event_list_ptr));	232	NEED_SUCCESS (WaitForEvents, (event_list_count, event_list_ptr));
127	}
128		233
129	PROTOTYPES: DISABLE	234	PROTOTYPES: DISABLE
130		235
131	MODULE = OpenCL PACKAGE = OpenCL::Platform	236	MODULE = OpenCL PACKAGE = OpenCL::Platform
132		237
133	void	238	void
134	info (OpenCL::Platform this, cl_platform_info name)	239	info (OpenCL::Platform this, cl_platform_info name)
135	PPCODE:	240	PPCODE:
136	INFO (Platform)	241	INFO (Platform)
137		242
		243	#BEGIN:platform
		244
		245	void
		246	profile (OpenCL::Platform this)
		247	PPCODE:
		248	size_t size;
		249	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_PROFILE, 0, 0, &size));
		250	char *value = tmpbuf (size);
		251	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_PROFILE, size, value, 0));
		252	int i, n = 1;
		253	EXTEND (SP, n);
		254	for (i = 0; i < n; ++i)
		255	PUSHs (sv_2mortal (newSVpv (value, 0)));
		256
		257	void
		258	version (OpenCL::Platform this)
		259	PPCODE:
		260	size_t size;
		261	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_VERSION, 0, 0, &size));
		262	char *value = tmpbuf (size);
		263	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_VERSION, size, value, 0));
		264	int i, n = 1;
		265	EXTEND (SP, n);
		266	for (i = 0; i < n; ++i)
		267	PUSHs (sv_2mortal (newSVpv (value, 0)));
		268
		269	void
		270	name (OpenCL::Platform this)
		271	PPCODE:
		272	size_t size;
		273	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_NAME, 0, 0, &size));
		274	char *value = tmpbuf (size);
		275	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_NAME, size, value, 0));
		276	int i, n = 1;
		277	EXTEND (SP, n);
		278	for (i = 0; i < n; ++i)
		279	PUSHs (sv_2mortal (newSVpv (value, 0)));
		280
		281	void
		282	vendor (OpenCL::Platform this)
		283	PPCODE:
		284	size_t size;
		285	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_VENDOR, 0, 0, &size));
		286	char *value = tmpbuf (size);
		287	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_VENDOR, size, value, 0));
		288	int i, n = 1;
		289	EXTEND (SP, n);
		290	for (i = 0; i < n; ++i)
		291	PUSHs (sv_2mortal (newSVpv (value, 0)));
		292
		293	void
		294	extensions (OpenCL::Platform this)
		295	PPCODE:
		296	size_t size;
		297	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_EXTENSIONS, 0, 0, &size));
		298	char *value = tmpbuf (size);
		299	NEED_SUCCESS (GetPlatformInfo, (this, CL_PLATFORM_EXTENSIONS, size, value, 0));
		300	int i, n = 1;
		301	EXTEND (SP, n);
		302	for (i = 0; i < n; ++i)
		303	PUSHs (sv_2mortal (newSVpv (value, 0)));
		304
		305	#END:platform
		306
138	void	307	void
139	devices (OpenCL::Platform this, cl_device_type type = CL_DEVICE_TYPE_ALL)	308	devices (OpenCL::Platform this, cl_device_type type = CL_DEVICE_TYPE_ALL)
140	PPCODE:	309	PPCODE:
141	{
142	cl_device_id *list;	310	cl_device_id *list;
143	cl_uint count;	311	cl_uint count;
144	int i;	312	int i;
145		313
146	NEED_SUCCESS (GetDeviceIDs, (this, type, 0, 0, &count));	314	NEED_SUCCESS (GetDeviceIDs, (this, type, 0, 0, &count));
147	Newx (list, count, cl_device_id);	315	list = tmpbuf (sizeof (*list) * count);
148	NEED_SUCCESS (GetDeviceIDs, (this, type, count, list, 0));	316	NEED_SUCCESS (GetDeviceIDs, (this, type, count, list, 0));
149		317
150	EXTEND (SP, count);	318	EXTEND (SP, count);
151	for (i = 0; i < count; ++i)	319	for (i = 0; i < count; ++i)
152	PUSHs (sv_setref_pv (sv_newmortal (), "OpenCL::Device", list [i]));	320	PUSHs (sv_setref_pv (sv_newmortal (), "OpenCL::Device", list [i]));
153		321
154	Safefree (list);
155	}
156
157	void	322	void
		323	context (OpenCL::Platform this, FUTURE properties, SV *devices, FUTURE notify = 0)
		324	PPCODE:
		325	if (!SvROK (devices) || SvTYPE (SvRV (devices)) != SVt_PVAV)
		326	croak ("OpenCL::Platform argument 'device' must be an arrayref with device objects, in call");
		327
		328	AV *av = (AV *)SvRV (devices);
		329	cl_uint num_devices = av_len (av) + 1;
		330	cl_device_id *device_list = tmpbuf (sizeof (cl_device_id) * num_devices);
		331	int i;
		332
		333	for (i = num_devices; i--; )
		334	device_list [i] = SvPTROBJ ("clCreateContext", "devices", *av_fetch (av, i, 0), "OpenCL::Device");
		335
		336	NEED_SUCCESS_ARG (cl_context ctx, CreateContext, (0, num_devices, device_list, 0, 0, &res));
		337	XPUSH_NEW_OBJ ("OpenCL::Context", ctx);
		338
		339	void
158	context_from_type_simple (OpenCL::Platform this, cl_device_type type = CL_DEVICE_TYPE_DEFAULT)	340	context_from_type (OpenCL::Platform this, FUTURE properties = 0, cl_device_type type = CL_DEVICE_TYPE_DEFAULT, FUTURE notify = 0)
159	PPCODE:	341	PPCODE:
160	{
161	cl_int res;
162	cl_context_properties props[] = { CL_CONTEXT_PLATFORM, (cl_context_properties)this, 0 };	342	cl_context_properties props[] = { CL_CONTEXT_PLATFORM, (cl_context_properties)this, 0 };
163	cl_context ctx = clCreateContextFromType (props, type, 0, 0, &res);	343	NEED_SUCCESS_ARG (cl_context ctx, CreateContextFromType, (props, type, 0, 0, &res));
164
165	if (res)
166	FAIL (CreateContextFromType, res);
167
168	XPUSH_NEW_OBJ ("OpenCL::Context", ctx);	344	XPUSH_NEW_OBJ ("OpenCL::Context", ctx);
169	}
170
171	void
172	unload_compiler ()
173	CODE:
174	NEED_SUCCESS (UnloadCompiler, ());
175		345
176	MODULE = OpenCL PACKAGE = OpenCL::Device	346	MODULE = OpenCL PACKAGE = OpenCL::Device
177		347
178	void	348	void
179	info (OpenCL::Device this, cl_device_info name)	349	info (OpenCL::Device this, cl_device_info name)
180	PPCODE:	350	PPCODE:
181	INFO (Device)	351	INFO (Device)
182		352
		353	#BEGIN:device
		354
183	void	355	void
184	context_simple (OpenCL::Device this)	356	type (OpenCL::Device this)
185	PPCODE:	357	PPCODE:
186	{	358	cl_device_type value [1];
187	cl_int res;	359	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_TYPE, sizeof (value), value, 0));
188	cl_context ctx = clCreateContext (0, 1, &this, 0, 0, &res);	360	EXTEND (SP, 1);
		361	const int i = 0;
		362	PUSHs (sv_2mortal (newSViv (value [i])));
189		363
190	if (res)	364	void
191	FAIL (CreateContext, res);	365	vendor_id (OpenCL::Device this)
		366	PPCODE:
		367	cl_uint value [1];
		368	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_VENDOR_ID, sizeof (value), value, 0));
		369	EXTEND (SP, 1);
		370	const int i = 0;
		371	PUSHs (sv_2mortal (newSVuv (value [i])));
192		372
193	XPUSH_NEW_OBJ ("OpenCL::Context", ctx);	373	void
194	}	374	max_compute_units (OpenCL::Device this)
		375	PPCODE:
		376	cl_uint value [1];
		377	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_COMPUTE_UNITS, sizeof (value), value, 0));
		378	EXTEND (SP, 1);
		379	const int i = 0;
		380	PUSHs (sv_2mortal (newSVuv (value [i])));
		381
		382	void
		383	max_work_item_dimensions (OpenCL::Device this)
		384	PPCODE:
		385	cl_uint value [1];
		386	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS, sizeof (value), value, 0));
		387	EXTEND (SP, 1);
		388	const int i = 0;
		389	PUSHs (sv_2mortal (newSVuv (value [i])));
		390
		391	void
		392	max_work_group_size (OpenCL::Device this)
		393	PPCODE:
		394	size_t value [1];
		395	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_WORK_GROUP_SIZE, sizeof (value), value, 0));
		396	EXTEND (SP, 1);
		397	const int i = 0;
		398	PUSHs (sv_2mortal (newSVuv (value [i])));
		399
		400	void
		401	max_work_item_sizes (OpenCL::Device this)
		402	PPCODE:
		403	size_t size;
		404	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_WORK_ITEM_SIZES, 0, 0, &size));
		405	size_t *value = tmpbuf (size);
		406	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_WORK_ITEM_SIZES, size, value, 0));
		407	int i, n = size / sizeof (value [0]);
		408	EXTEND (SP, n);
		409	for (i = 0; i < n; ++i)
		410	PUSHs (sv_2mortal (newSVuv (value [i])));
		411
		412	void
		413	preferred_vector_width_char (OpenCL::Device this)
		414	PPCODE:
		415	cl_uint value [1];
		416	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR, sizeof (value), value, 0));
		417	EXTEND (SP, 1);
		418	const int i = 0;
		419	PUSHs (sv_2mortal (newSVuv (value [i])));
		420
		421	void
		422	preferred_vector_width_short (OpenCL::Device this)
		423	PPCODE:
		424	cl_uint value [1];
		425	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT, sizeof (value), value, 0));
		426	EXTEND (SP, 1);
		427	const int i = 0;
		428	PUSHs (sv_2mortal (newSVuv (value [i])));
		429
		430	void
		431	preferred_vector_width_int (OpenCL::Device this)
		432	PPCODE:
		433	cl_uint value [1];
		434	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT, sizeof (value), value, 0));
		435	EXTEND (SP, 1);
		436	const int i = 0;
		437	PUSHs (sv_2mortal (newSVuv (value [i])));
		438
		439	void
		440	preferred_vector_width_long (OpenCL::Device this)
		441	PPCODE:
		442	cl_uint value [1];
		443	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG, sizeof (value), value, 0));
		444	EXTEND (SP, 1);
		445	const int i = 0;
		446	PUSHs (sv_2mortal (newSVuv (value [i])));
		447
		448	void
		449	preferred_vector_width_float (OpenCL::Device this)
		450	PPCODE:
		451	cl_uint value [1];
		452	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT, sizeof (value), value, 0));
		453	EXTEND (SP, 1);
		454	const int i = 0;
		455	PUSHs (sv_2mortal (newSVuv (value [i])));
		456
		457	void
		458	preferred_vector_width_double (OpenCL::Device this)
		459	PPCODE:
		460	cl_uint value [1];
		461	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE, sizeof (value), value, 0));
		462	EXTEND (SP, 1);
		463	const int i = 0;
		464	PUSHs (sv_2mortal (newSVuv (value [i])));
		465
		466	void
		467	max_clock_frequency (OpenCL::Device this)
		468	PPCODE:
		469	cl_uint value [1];
		470	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_CLOCK_FREQUENCY, sizeof (value), value, 0));
		471	EXTEND (SP, 1);
		472	const int i = 0;
		473	PUSHs (sv_2mortal (newSVuv (value [i])));
		474
		475	void
		476	address_bits (OpenCL::Device this)
		477	PPCODE:
		478	cl_bitfield value [1];
		479	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_ADDRESS_BITS, sizeof (value), value, 0));
		480	EXTEND (SP, 1);
		481	const int i = 0;
		482	PUSHs (sv_2mortal (newSVuv (value [i])));
		483
		484	void
		485	max_read_image_args (OpenCL::Device this)
		486	PPCODE:
		487	cl_uint value [1];
		488	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_READ_IMAGE_ARGS, sizeof (value), value, 0));
		489	EXTEND (SP, 1);
		490	const int i = 0;
		491	PUSHs (sv_2mortal (newSVuv (value [i])));
		492
		493	void
		494	max_write_image_args (OpenCL::Device this)
		495	PPCODE:
		496	cl_uint value [1];
		497	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_WRITE_IMAGE_ARGS, sizeof (value), value, 0));
		498	EXTEND (SP, 1);
		499	const int i = 0;
		500	PUSHs (sv_2mortal (newSVuv (value [i])));
		501
		502	void
		503	max_mem_alloc_size (OpenCL::Device this)
		504	PPCODE:
		505	cl_ulong value [1];
		506	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_MEM_ALLOC_SIZE, sizeof (value), value, 0));
		507	EXTEND (SP, 1);
		508	const int i = 0;
		509	PUSHs (sv_2mortal (newSVuv (value [i])));
		510
		511	void
		512	image2d_max_width (OpenCL::Device this)
		513	PPCODE:
		514	size_t value [1];
		515	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE2D_MAX_WIDTH, sizeof (value), value, 0));
		516	EXTEND (SP, 1);
		517	const int i = 0;
		518	PUSHs (sv_2mortal (newSVuv (value [i])));
		519
		520	void
		521	image2d_max_height (OpenCL::Device this)
		522	PPCODE:
		523	size_t value [1];
		524	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE2D_MAX_HEIGHT, sizeof (value), value, 0));
		525	EXTEND (SP, 1);
		526	const int i = 0;
		527	PUSHs (sv_2mortal (newSVuv (value [i])));
		528
		529	void
		530	image3d_max_width (OpenCL::Device this)
		531	PPCODE:
		532	size_t value [1];
		533	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE3D_MAX_WIDTH, sizeof (value), value, 0));
		534	EXTEND (SP, 1);
		535	const int i = 0;
		536	PUSHs (sv_2mortal (newSVuv (value [i])));
		537
		538	void
		539	image3d_max_height (OpenCL::Device this)
		540	PPCODE:
		541	size_t value [1];
		542	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE3D_MAX_HEIGHT, sizeof (value), value, 0));
		543	EXTEND (SP, 1);
		544	const int i = 0;
		545	PUSHs (sv_2mortal (newSVuv (value [i])));
		546
		547	void
		548	image3d_max_depth (OpenCL::Device this)
		549	PPCODE:
		550	size_t value [1];
		551	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE3D_MAX_DEPTH, sizeof (value), value, 0));
		552	EXTEND (SP, 1);
		553	const int i = 0;
		554	PUSHs (sv_2mortal (newSVuv (value [i])));
		555
		556	void
		557	image_support (OpenCL::Device this)
		558	PPCODE:
		559	cl_uint value [1];
		560	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_IMAGE_SUPPORT, sizeof (value), value, 0));
		561	EXTEND (SP, 1);
		562	const int i = 0;
		563	PUSHs (sv_2mortal (newSVuv (value [i])));
		564
		565	void
		566	max_parameter_size (OpenCL::Device this)
		567	PPCODE:
		568	size_t value [1];
		569	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_PARAMETER_SIZE, sizeof (value), value, 0));
		570	EXTEND (SP, 1);
		571	const int i = 0;
		572	PUSHs (sv_2mortal (newSVuv (value [i])));
		573
		574	void
		575	max_samplers (OpenCL::Device this)
		576	PPCODE:
		577	cl_uint value [1];
		578	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_SAMPLERS, sizeof (value), value, 0));
		579	EXTEND (SP, 1);
		580	const int i = 0;
		581	PUSHs (sv_2mortal (newSVuv (value [i])));
		582
		583	void
		584	mem_base_addr_align (OpenCL::Device this)
		585	PPCODE:
		586	cl_uint value [1];
		587	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MEM_BASE_ADDR_ALIGN, sizeof (value), value, 0));
		588	EXTEND (SP, 1);
		589	const int i = 0;
		590	PUSHs (sv_2mortal (newSVuv (value [i])));
		591
		592	void
		593	min_data_type_align_size (OpenCL::Device this)
		594	PPCODE:
		595	cl_uint value [1];
		596	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE, sizeof (value), value, 0));
		597	EXTEND (SP, 1);
		598	const int i = 0;
		599	PUSHs (sv_2mortal (newSVuv (value [i])));
		600
		601	void
		602	single_fp_config (OpenCL::Device this)
		603	PPCODE:
		604	cl_device_fp_config value [1];
		605	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_SINGLE_FP_CONFIG, sizeof (value), value, 0));
		606	EXTEND (SP, 1);
		607	const int i = 0;
		608	PUSHs (sv_2mortal (newSVuv (value [i])));
		609
		610	void
		611	global_mem_cache_type (OpenCL::Device this)
		612	PPCODE:
		613	cl_device_mem_cache_type value [1];
		614	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_GLOBAL_MEM_CACHE_TYPE, sizeof (value), value, 0));
		615	EXTEND (SP, 1);
		616	const int i = 0;
		617	PUSHs (sv_2mortal (newSVuv (value [i])));
		618
		619	void
		620	global_mem_cacheline_size (OpenCL::Device this)
		621	PPCODE:
		622	cl_uint value [1];
		623	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE, sizeof (value), value, 0));
		624	EXTEND (SP, 1);
		625	const int i = 0;
		626	PUSHs (sv_2mortal (newSVuv (value [i])));
		627
		628	void
		629	global_mem_cache_size (OpenCL::Device this)
		630	PPCODE:
		631	cl_ulong value [1];
		632	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_GLOBAL_MEM_CACHE_SIZE, sizeof (value), value, 0));
		633	EXTEND (SP, 1);
		634	const int i = 0;
		635	PUSHs (sv_2mortal (newSVuv (value [i])));
		636
		637	void
		638	global_mem_size (OpenCL::Device this)
		639	PPCODE:
		640	cl_ulong value [1];
		641	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_GLOBAL_MEM_SIZE, sizeof (value), value, 0));
		642	EXTEND (SP, 1);
		643	const int i = 0;
		644	PUSHs (sv_2mortal (newSVuv (value [i])));
		645
		646	void
		647	max_constant_buffer_size (OpenCL::Device this)
		648	PPCODE:
		649	cl_ulong value [1];
		650	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE, sizeof (value), value, 0));
		651	EXTEND (SP, 1);
		652	const int i = 0;
		653	PUSHs (sv_2mortal (newSVuv (value [i])));
		654
		655	void
		656	max_constant_args (OpenCL::Device this)
		657	PPCODE:
		658	cl_uint value [1];
		659	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_MAX_CONSTANT_ARGS, sizeof (value), value, 0));
		660	EXTEND (SP, 1);
		661	const int i = 0;
		662	PUSHs (sv_2mortal (newSVuv (value [i])));
		663
		664	void
		665	local_mem_type (OpenCL::Device this)
		666	PPCODE:
		667	cl_device_local_mem_type value [1];
		668	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_LOCAL_MEM_TYPE, sizeof (value), value, 0));
		669	EXTEND (SP, 1);
		670	const int i = 0;
		671	PUSHs (sv_2mortal (newSVuv (value [i])));
		672
		673	void
		674	local_mem_size (OpenCL::Device this)
		675	PPCODE:
		676	cl_ulong value [1];
		677	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_LOCAL_MEM_SIZE, sizeof (value), value, 0));
		678	EXTEND (SP, 1);
		679	const int i = 0;
		680	PUSHs (sv_2mortal (newSVuv (value [i])));
		681
		682	void
		683	error_correction_support (OpenCL::Device this)
		684	PPCODE:
		685	cl_bool value [1];
		686	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_ERROR_CORRECTION_SUPPORT, sizeof (value), value, 0));
		687	EXTEND (SP, 1);
		688	const int i = 0;
		689	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		690
		691	void
		692	profiling_timer_resolution (OpenCL::Device this)
		693	PPCODE:
		694	size_t value [1];
		695	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PROFILING_TIMER_RESOLUTION, sizeof (value), value, 0));
		696	EXTEND (SP, 1);
		697	const int i = 0;
		698	PUSHs (sv_2mortal (newSVuv (value [i])));
		699
		700	void
		701	endian_little (OpenCL::Device this)
		702	PPCODE:
		703	cl_bool value [1];
		704	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_ENDIAN_LITTLE, sizeof (value), value, 0));
		705	EXTEND (SP, 1);
		706	const int i = 0;
		707	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		708
		709	void
		710	available (OpenCL::Device this)
		711	PPCODE:
		712	cl_bool value [1];
		713	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_AVAILABLE, sizeof (value), value, 0));
		714	EXTEND (SP, 1);
		715	const int i = 0;
		716	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		717
		718	void
		719	compiler_available (OpenCL::Device this)
		720	PPCODE:
		721	cl_bool value [1];
		722	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_COMPILER_AVAILABLE, sizeof (value), value, 0));
		723	EXTEND (SP, 1);
		724	const int i = 0;
		725	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		726
		727	void
		728	execution_capabilities (OpenCL::Device this)
		729	PPCODE:
		730	cl_device_exec_capabilities value [1];
		731	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_EXECUTION_CAPABILITIES, sizeof (value), value, 0));
		732	EXTEND (SP, 1);
		733	const int i = 0;
		734	PUSHs (sv_2mortal (newSVuv (value [i])));
		735
		736	void
		737	properties (OpenCL::Device this)
		738	PPCODE:
		739	cl_command_queue_properties value [1];
		740	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_QUEUE_PROPERTIES, sizeof (value), value, 0));
		741	EXTEND (SP, 1);
		742	const int i = 0;
		743	PUSHs (sv_2mortal (newSViv (value [i])));
		744
		745	void
		746	platform (OpenCL::Device this)
		747	PPCODE:
		748	cl_platform_id value [1];
		749	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PLATFORM, sizeof (value), value, 0));
		750	EXTEND (SP, 1);
		751	const int i = 0;
		752	{
		753	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Platform", value [i]));
		754	}
		755
		756	void
		757	name (OpenCL::Device this)
		758	PPCODE:
		759	size_t size;
		760	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NAME, 0, 0, &size));
		761	char *value = tmpbuf (size);
		762	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NAME, size, value, 0));
		763	int i, n = 1;
		764	EXTEND (SP, n);
		765	for (i = 0; i < n; ++i)
		766	PUSHs (sv_2mortal (newSVpv (value, 0)));
		767
		768	void
		769	vendor (OpenCL::Device this)
		770	PPCODE:
		771	size_t size;
		772	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_VENDOR, 0, 0, &size));
		773	char *value = tmpbuf (size);
		774	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_VENDOR, size, value, 0));
		775	int i, n = 1;
		776	EXTEND (SP, n);
		777	for (i = 0; i < n; ++i)
		778	PUSHs (sv_2mortal (newSVpv (value, 0)));
		779
		780	void
		781	driver_version (OpenCL::Device this)
		782	PPCODE:
		783	size_t size;
		784	NEED_SUCCESS (GetDeviceInfo, (this, CL_DRIVER_VERSION, 0, 0, &size));
		785	char *value = tmpbuf (size);
		786	NEED_SUCCESS (GetDeviceInfo, (this, CL_DRIVER_VERSION, size, value, 0));
		787	int i, n = 1;
		788	EXTEND (SP, n);
		789	for (i = 0; i < n; ++i)
		790	PUSHs (sv_2mortal (newSVpv (value, 0)));
		791
		792	void
		793	profile (OpenCL::Device this)
		794	PPCODE:
		795	size_t size;
		796	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PROFILE, 0, 0, &size));
		797	char *value = tmpbuf (size);
		798	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PROFILE, size, value, 0));
		799	int i, n = 1;
		800	EXTEND (SP, n);
		801	for (i = 0; i < n; ++i)
		802	PUSHs (sv_2mortal (newSVpv (value, 0)));
		803
		804	void
		805	version (OpenCL::Device this)
		806	PPCODE:
		807	size_t size;
		808	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_VERSION, 0, 0, &size));
		809	char *value = tmpbuf (size);
		810	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_VERSION, size, value, 0));
		811	int i, n = 1;
		812	EXTEND (SP, n);
		813	for (i = 0; i < n; ++i)
		814	PUSHs (sv_2mortal (newSVpv (value, 0)));
		815
		816	void
		817	extensions (OpenCL::Device this)
		818	PPCODE:
		819	size_t size;
		820	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_EXTENSIONS, 0, 0, &size));
		821	char *value = tmpbuf (size);
		822	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_EXTENSIONS, size, value, 0));
		823	int i, n = 1;
		824	EXTEND (SP, n);
		825	for (i = 0; i < n; ++i)
		826	PUSHs (sv_2mortal (newSVpv (value, 0)));
		827
		828	void
		829	preferred_vector_width_half (OpenCL::Device this)
		830	PPCODE:
		831	cl_uint value [1];
		832	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PREFERRED_VECTOR_WIDTH_HALF, sizeof (value), value, 0));
		833	EXTEND (SP, 1);
		834	const int i = 0;
		835	PUSHs (sv_2mortal (newSVuv (value [i])));
		836
		837	void
		838	native_vector_width_char (OpenCL::Device this)
		839	PPCODE:
		840	cl_uint value [1];
		841	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR, sizeof (value), value, 0));
		842	EXTEND (SP, 1);
		843	const int i = 0;
		844	PUSHs (sv_2mortal (newSVuv (value [i])));
		845
		846	void
		847	native_vector_width_short (OpenCL::Device this)
		848	PPCODE:
		849	cl_uint value [1];
		850	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT, sizeof (value), value, 0));
		851	EXTEND (SP, 1);
		852	const int i = 0;
		853	PUSHs (sv_2mortal (newSVuv (value [i])));
		854
		855	void
		856	native_vector_width_int (OpenCL::Device this)
		857	PPCODE:
		858	cl_uint value [1];
		859	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_INT, sizeof (value), value, 0));
		860	EXTEND (SP, 1);
		861	const int i = 0;
		862	PUSHs (sv_2mortal (newSVuv (value [i])));
		863
		864	void
		865	native_vector_width_long (OpenCL::Device this)
		866	PPCODE:
		867	cl_uint value [1];
		868	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG, sizeof (value), value, 0));
		869	EXTEND (SP, 1);
		870	const int i = 0;
		871	PUSHs (sv_2mortal (newSVuv (value [i])));
		872
		873	void
		874	native_vector_width_float (OpenCL::Device this)
		875	PPCODE:
		876	cl_uint value [1];
		877	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT, sizeof (value), value, 0));
		878	EXTEND (SP, 1);
		879	const int i = 0;
		880	PUSHs (sv_2mortal (newSVuv (value [i])));
		881
		882	void
		883	native_vector_width_double (OpenCL::Device this)
		884	PPCODE:
		885	cl_uint value [1];
		886	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE, sizeof (value), value, 0));
		887	EXTEND (SP, 1);
		888	const int i = 0;
		889	PUSHs (sv_2mortal (newSVuv (value [i])));
		890
		891	void
		892	native_vector_width_half (OpenCL::Device this)
		893	PPCODE:
		894	cl_uint value [1];
		895	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_NATIVE_VECTOR_WIDTH_HALF, sizeof (value), value, 0));
		896	EXTEND (SP, 1);
		897	const int i = 0;
		898	PUSHs (sv_2mortal (newSVuv (value [i])));
		899
		900	void
		901	double_fp_config (OpenCL::Device this)
		902	PPCODE:
		903	cl_device_fp_config value [1];
		904	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_DOUBLE_FP_CONFIG, sizeof (value), value, 0));
		905	EXTEND (SP, 1);
		906	const int i = 0;
		907	PUSHs (sv_2mortal (newSVuv (value [i])));
		908
		909	void
		910	half_fp_config (OpenCL::Device this)
		911	PPCODE:
		912	cl_device_fp_config value [1];
		913	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_HALF_FP_CONFIG, sizeof (value), value, 0));
		914	EXTEND (SP, 1);
		915	const int i = 0;
		916	PUSHs (sv_2mortal (newSVuv (value [i])));
		917
		918	void
		919	host_unified_memory (OpenCL::Device this)
		920	PPCODE:
		921	cl_bool value [1];
		922	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_HOST_UNIFIED_MEMORY, sizeof (value), value, 0));
		923	EXTEND (SP, 1);
		924	const int i = 0;
		925	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		926
		927	void
		928	parent_device_ext (OpenCL::Device this)
		929	PPCODE:
		930	cl_device_id value [1];
		931	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PARENT_DEVICE_EXT, sizeof (value), value, 0));
		932	EXTEND (SP, 1);
		933	const int i = 0;
		934	{
		935	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Device", value [i]));
		936	}
		937
		938	void
		939	partition_types_ext (OpenCL::Device this)
		940	PPCODE:
		941	size_t size;
		942	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PARTITION_TYPES_EXT, 0, 0, &size));
		943	cl_device_partition_property_ext *value = tmpbuf (size);
		944	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PARTITION_TYPES_EXT, size, value, 0));
		945	int i, n = size / sizeof (value [0]);
		946	EXTEND (SP, n);
		947	for (i = 0; i < n; ++i)
		948	PUSHs (sv_2mortal (newSVuv (value [i])));
		949
		950	void
		951	affinity_domains_ext (OpenCL::Device this)
		952	PPCODE:
		953	size_t size;
		954	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_AFFINITY_DOMAINS_EXT, 0, 0, &size));
		955	cl_device_partition_property_ext *value = tmpbuf (size);
		956	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_AFFINITY_DOMAINS_EXT, size, value, 0));
		957	int i, n = size / sizeof (value [0]);
		958	EXTEND (SP, n);
		959	for (i = 0; i < n; ++i)
		960	PUSHs (sv_2mortal (newSVuv (value [i])));
		961
		962	void
		963	reference_count_ext (OpenCL::Device this)
		964	PPCODE:
		965	cl_uint value [1];
		966	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_REFERENCE_COUNT_EXT , sizeof (value), value, 0));
		967	EXTEND (SP, 1);
		968	const int i = 0;
		969	PUSHs (sv_2mortal (newSVuv (value [i])));
		970
		971	void
		972	partition_style_ext (OpenCL::Device this)
		973	PPCODE:
		974	size_t size;
		975	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PARTITION_STYLE_EXT, 0, 0, &size));
		976	cl_device_partition_property_ext *value = tmpbuf (size);
		977	NEED_SUCCESS (GetDeviceInfo, (this, CL_DEVICE_PARTITION_STYLE_EXT, size, value, 0));
		978	int i, n = size / sizeof (value [0]);
		979	EXTEND (SP, n);
		980	for (i = 0; i < n; ++i)
		981	PUSHs (sv_2mortal (newSVuv (value [i])));
		982
		983	#END:device
195		984
196	MODULE = OpenCL PACKAGE = OpenCL::Context	985	MODULE = OpenCL PACKAGE = OpenCL::Context
197		986
198	void	987	void
199	DESTROY (OpenCL::Context context)	988	DESTROY (OpenCL::Context context)
…		…
204	info (OpenCL::Context this, cl_context_info name)	993	info (OpenCL::Context this, cl_context_info name)
205	PPCODE:	994	PPCODE:
206	INFO (Context)	995	INFO (Context)
207		996
208	void	997	void
209	command_queue_simple (OpenCL::Context this, OpenCL::Device device)	998	queue (OpenCL::Context this, OpenCL::Device device, cl_command_queue_properties properties = 0)
210	PPCODE:	999	PPCODE:
211	{
212	cl_int res;
213	cl_command_queue queue = clCreateCommandQueue (this, device, 0, &res);	1000	NEED_SUCCESS_ARG (cl_command_queue queue, CreateCommandQueue, (this, device, properties, &res));
214
215	if (res)
216	FAIL (CreateCommandQueue, res);
217
218	XPUSH_NEW_OBJ ("OpenCL::Queue", queue);	1001	XPUSH_NEW_OBJ ("OpenCL::Queue", queue);
219	}	1002
		1003	void
		1004	user_event (OpenCL::Context this)
		1005	PPCODE:
		1006	NEED_SUCCESS_ARG (cl_event ev, CreateUserEvent, (this, &res));
		1007	XPUSH_NEW_OBJ ("OpenCL::UserEvent", ev);
220		1008
221	void	1009	void
222	buffer (OpenCL::Context this, cl_mem_flags flags, size_t len)	1010	buffer (OpenCL::Context this, cl_mem_flags flags, size_t len)
223	PPCODE:	1011	PPCODE:
224	{	1012	if (flags & (CL_MEM_USE_HOST_PTR | CL_MEM_COPY_HOST_PTR))
225	cl_int res;	1013	croak ("clCreateBuffer: cannot use/copy host ptr when no data is given, use $context->buffer_sv instead?");
		1014
226	cl_mem mem = clCreateBuffer (this, flags, len, 0, &res);	1015	NEED_SUCCESS_ARG (cl_mem mem, CreateBuffer, (this, flags, len, 0, &res));
227
228	if (res)
229	FAIL (CreateBuffer, res);
230
231	XPUSH_NEW_OBJ ("OpenCL::Memory", mem);	1016	XPUSH_NEW_OBJ ("OpenCL::Buffer", mem);
232	}
233		1017
234	void	1018	void
235	buffer_sv (OpenCL::Context this, cl_mem_flags flags, SV *data)	1019	buffer_sv (OpenCL::Context this, cl_mem_flags flags, SV *data)
236	PPCODE:	1020	PPCODE:
237	{
238	STRLEN len;	1021	STRLEN len;
239	char *ptr = SvPVbyte (data, len);	1022	char *ptr = SvPVbyte (data, len);
240	cl_int res;	1023
		1024	if (!(flags & (CL_MEM_USE_HOST_PTR | CL_MEM_COPY_HOST_PTR)))
		1025	croak ("clCreateBuffer: have to specify use or copy host ptr when buffer data is given, use $context->buffer instead?");
		1026
241	cl_mem mem = clCreateBuffer (this, flags, len, ptr, &res);	1027	NEED_SUCCESS_ARG (cl_mem mem, CreateBuffer, (this, flags, len, ptr, &res));
242
243	if (res)
244	FAIL (CreateBuffer, res);
245
246	XPUSH_NEW_OBJ ("OpenCL::Memory", mem);	1028	XPUSH_NEW_OBJ ("OpenCL::Buffer", mem);
		1029
		1030	void
		1031	image2d (OpenCL::Context this, cl_mem_flags flags, cl_channel_order channel_order, cl_channel_type channel_type, size_t width, size_t height, size_t row_pitch = 0, SV *data = &PL_sv_undef)
		1032	PPCODE:
		1033	STRLEN len;
		1034	char *ptr = SvPVbyte (data, len);
		1035	const cl_image_format format = { channel_order, channel_type };
		1036	NEED_SUCCESS_ARG (cl_mem mem, CreateImage2D, (this, flags, &format, width, height, row_pitch, ptr, &res));
		1037	XPUSH_NEW_OBJ ("OpenCL::Image2D", mem);
		1038
		1039	void
		1040	image3d (OpenCL::Context this, cl_mem_flags flags, cl_channel_order channel_order, cl_channel_type channel_type, size_t width, size_t height, size_t depth, size_t row_pitch = 0, size_t slice_pitch = 0, SV *data = &PL_sv_undef)
		1041	PPCODE:
		1042	STRLEN len;
		1043	char *ptr = SvPVbyte (data, len);
		1044	const cl_image_format format = { channel_order, channel_type };
		1045	NEED_SUCCESS_ARG (cl_mem mem, CreateImage3D, (this, flags, &format, width, height, depth, row_pitch, slice_pitch, ptr, &res));
		1046	XPUSH_NEW_OBJ ("OpenCL::Image3D", mem);
		1047
		1048	void
		1049	supported_image_formats (OpenCL::Context this, cl_mem_flags flags, cl_mem_object_type image_type)
		1050	PPCODE:
		1051	{
		1052	cl_uint count;
		1053	cl_image_format *list;
		1054	int i;
		1055
		1056	NEED_SUCCESS (GetSupportedImageFormats, (this, flags, image_type, 0, 0, &count));
		1057	Newx (list, count, cl_image_format);
		1058	NEED_SUCCESS (GetSupportedImageFormats, (this, flags, image_type, count, list, 0));
		1059
		1060	EXTEND (SP, count);
		1061	for (i = 0; i < count; ++i)
		1062	{
		1063	AV *av = newAV ();
		1064	av_store (av, 1, newSVuv (list [i].image_channel_data_type));
		1065	av_store (av, 0, newSVuv (list [i].image_channel_order));
		1066	PUSHs (sv_2mortal (newRV_noinc ((SV *)av)));
		1067	}
247	}	1068	}
248		1069
249	void	1070	void
250	sampler (OpenCL::Context this, cl_bool normalized_coords, cl_addressing_mode addressing_mode, cl_filter_mode filter_mode)	1071	sampler (OpenCL::Context this, cl_bool normalized_coords, cl_addressing_mode addressing_mode, cl_filter_mode filter_mode)
251	PPCODE:	1072	PPCODE:
252	{
253	cl_int res;
254	cl_sampler sampler = clCreateSampler (this, normalized_coords, addressing_mode, filter_mode, &res);	1073	NEED_SUCCESS_ARG (cl_sampler sampler, CreateSampler, (this, normalized_coords, addressing_mode, filter_mode, &res));
255
256	if (res)
257	FAIL (CreateSampler, res);
258
259	XPUSH_NEW_OBJ ("OpenCL::Sampler", sampler);	1074	XPUSH_NEW_OBJ ("OpenCL::Sampler", sampler);
260	}
261		1075
262	void	1076	void
263	program_with_source (OpenCL::Context this, SV *program)	1077	program_with_source (OpenCL::Context this, SV *program)
264	PPCODE:	1078	PPCODE:
265	{
266	STRLEN len;	1079	STRLEN len;
267	size_t len2;	1080	size_t len2;
268	const char *ptr = SvPVbyte (program, len);	1081	const char *ptr = SvPVbyte (program, len);
269	cl_int res;
270	cl_program prog;
271		1082
272	len2 = len;	1083	len2 = len;
273	prog = clCreateProgramWithSource (this, 1, &ptr, &len2, &res);	1084	NEED_SUCCESS_ARG (cl_program prog, CreateProgramWithSource, (this, 1, &ptr, &len2, &res));
274
275	if (res)
276	FAIL (CreateProgramWithSource, res);
277
278	XPUSH_NEW_OBJ ("OpenCL::Program", prog);	1085	XPUSH_NEW_OBJ ("OpenCL::Program", prog);
279	}	1086
		1087	#BEGIN:context
		1088
		1089	void
		1090	reference_count (OpenCL::Context this)
		1091	PPCODE:
		1092	cl_uint value [1];
		1093	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_REFERENCE_COUNT, sizeof (value), value, 0));
		1094	EXTEND (SP, 1);
		1095	const int i = 0;
		1096	PUSHs (sv_2mortal (newSVuv (value [i])));
		1097
		1098	void
		1099	devices (OpenCL::Context this)
		1100	PPCODE:
		1101	size_t size;
		1102	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_DEVICES, 0, 0, &size));
		1103	cl_device_id *value = tmpbuf (size);
		1104	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_DEVICES, size, value, 0));
		1105	int i, n = size / sizeof (value [0]);
		1106	EXTEND (SP, n);
		1107	for (i = 0; i < n; ++i)
		1108	{
		1109	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Device", value [i]));
		1110	}
		1111
		1112	void
		1113	properties (OpenCL::Context this)
		1114	PPCODE:
		1115	size_t size;
		1116	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_PROPERTIES, 0, 0, &size));
		1117	cl_context_properties *value = tmpbuf (size);
		1118	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_PROPERTIES, size, value, 0));
		1119	int i, n = size / sizeof (value [0]);
		1120	EXTEND (SP, n);
		1121	for (i = 0; i < n; ++i)
		1122	PUSHs (sv_2mortal (newSVuv ((UV)value [i])));
		1123
		1124	void
		1125	num_devices (OpenCL::Context this)
		1126	PPCODE:
		1127	cl_uint value [1];
		1128	NEED_SUCCESS (GetContextInfo, (this, CL_CONTEXT_NUM_DEVICES, sizeof (value), value, 0));
		1129	EXTEND (SP, 1);
		1130	const int i = 0;
		1131	PUSHs (sv_2mortal (newSVuv (value [i])));
		1132
		1133	#END:context
280		1134
281	MODULE = OpenCL PACKAGE = OpenCL::Queue	1135	MODULE = OpenCL PACKAGE = OpenCL::Queue
282		1136
283	void	1137	void
284	DESTROY (OpenCL::Queue this)	1138	DESTROY (OpenCL::Queue this)
285	CODE:	1139	CODE:
286	clReleaseCommandQueue (this);	1140	clReleaseCommandQueue (this);
287		1141
288	void	1142	void
289	info (OpenCL::Queue this, cl_command_queue_info name)
290	PPCODE:
291	INFO (CommandQueue)
292
293	void
294	enqueue_read_buffer (OpenCL::Queue this, OpenCL::Memory mem, cl_bool blocking, size_t offset, size_t len, SV *data, ...)	1143	enqueue_read_buffer (OpenCL::Queue this, OpenCL::Buffer mem, cl_bool blocking, size_t offset, size_t len, SV *data, ...)
295	PPCODE:	1144	PPCODE:
296	{
297	cl_event ev = 0;	1145	cl_event ev = 0;
298	EVENT_LIST (6, items - 6);	1146	EVENT_LIST (6, items - 6);
299		1147
300	SvUPGRADE (data, SVt_PV);	1148	SvUPGRADE (data, SVt_PV);
301	SvGROW (data, len);	1149	SvGROW (data, len);
…		…
303	SvCUR_set (data, len);	1151	SvCUR_set (data, len);
304	NEED_SUCCESS (EnqueueReadBuffer, (this, mem, blocking, offset, len, SvPVX (data), event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));	1152	NEED_SUCCESS (EnqueueReadBuffer, (this, mem, blocking, offset, len, SvPVX (data), event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
305		1153
306	if (ev)	1154	if (ev)
307	XPUSH_NEW_OBJ ("OpenCL::Event", ev);	1155	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
308	}
309		1156
310	void	1157	void
311	enqueue_write_buffer (OpenCL::Queue this, OpenCL::Memory mem, cl_bool blocking, size_t offset, SV *data, ...)	1158	enqueue_write_buffer (OpenCL::Queue this, OpenCL::Buffer mem, cl_bool blocking, size_t offset, SV *data, ...)
312	PPCODE:	1159	PPCODE:
313	{
314	cl_event ev = 0;	1160	cl_event ev = 0;
315	STRLEN len;	1161	STRLEN len;
316	char *ptr = SvPVbyte (data, len);	1162	char *ptr = SvPVbyte (data, len);
317	EVENT_LIST (5, items - 5);	1163	EVENT_LIST (5, items - 5);
318		1164
319	NEED_SUCCESS (EnqueueReadBuffer, (this, mem, blocking, offset, len, ptr, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));	1165	NEED_SUCCESS (EnqueueReadBuffer, (this, mem, blocking, offset, len, ptr, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
320		1166
321	if (ev)	1167	if (ev)
322	XPUSH_NEW_OBJ ("OpenCL::Event", ev);	1168	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
323	}
324		1169
325	void	1170	void
326	enqueue_copy_buffer (OpenCL::Queue this, OpenCL::Memory src, OpenCL::Memory dst, size_t src_offset, size_t dst_offset, size_t len, ...)	1171	enqueue_copy_buffer (OpenCL::Queue this, OpenCL::Buffer src, OpenCL::Buffer dst, size_t src_offset, size_t dst_offset, size_t len, ...)
327	PPCODE:	1172	PPCODE:
328	{
329	cl_event ev = 0;	1173	cl_event ev = 0;
330	EVENT_LIST (6, items - 6);	1174	EVENT_LIST (6, items - 6);
331		1175
332	NEED_SUCCESS (EnqueueCopyBuffer, (this, src, dst, src_offset, dst_offset, len, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));	1176	NEED_SUCCESS (EnqueueCopyBuffer, (this, src, dst, src_offset, dst_offset, len, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
333		1177
334	if (ev)	1178	if (ev)
335	XPUSH_NEW_OBJ ("OpenCL::Event", ev);	1179	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
336	}	1180
		1181	void
		1182	enqueue_read_image (OpenCL::Queue this, OpenCL::Image src, cl_bool blocking, size_t src_x, size_t src_y, size_t src_z, size_t width, size_t height, size_t depth, size_t row_pitch, size_t slice_pitch, SV *data, ...)
		1183	PPCODE:
		1184	cl_event ev = 0;
		1185	const size_t src_origin[3] = { src_x, src_y, src_z };
		1186	const size_t region[3] = { width, height, depth };
		1187	EVENT_LIST (12, items - 12);
		1188
		1189	if (!row_pitch)
		1190	row_pitch = img_row_pitch (src);
		1191
		1192	if (depth > 1 && !slice_pitch)
		1193	slice_pitch = row_pitch * height;
		1194
		1195	size_t len = slice_pitch ? slice_pitch * depth : row_pitch * height;
		1196
		1197	SvUPGRADE (data, SVt_PV);
		1198	SvGROW (data, len);
		1199	SvPOK_only (data);
		1200	SvCUR_set (data, len);
		1201	NEED_SUCCESS (EnqueueReadImage, (this, src, blocking, src_origin, region, row_pitch, slice_pitch, SvPVX (data), event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1202
		1203	if (ev)
		1204	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1205
		1206	void
		1207	enqueue_write_image (OpenCL::Queue this, OpenCL::Image dst, cl_bool blocking, size_t dst_x, size_t dst_y, size_t dst_z, size_t width, size_t height, size_t depth, size_t row_pitch, size_t slice_pitch, SV *data, ...)
		1208	PPCODE:
		1209	cl_event ev = 0;
		1210	const size_t dst_origin[3] = { dst_x, dst_y, dst_z };
		1211	const size_t region[3] = { width, height, depth };
		1212	STRLEN len;
		1213	char *ptr = SvPVbyte (data, len);
		1214	EVENT_LIST (12, items - 12);
		1215
		1216	if (!row_pitch)
		1217	row_pitch = img_row_pitch (dst);
		1218
		1219	if (depth > 1 && !slice_pitch)
		1220	slice_pitch = row_pitch * height;
		1221
		1222	size_t min_len = slice_pitch ? slice_pitch * depth : row_pitch * height;
		1223
		1224	if (len < min_len)
		1225	croak ("clEnqueueWriteImage: data string is shorter than what would be transferred");
		1226
		1227	NEED_SUCCESS (EnqueueWriteImage, (this, dst, blocking, dst_origin, region, row_pitch, slice_pitch, SvPVX (data), event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1228
		1229	if (ev)
		1230	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1231
		1232	void
		1233	enqueue_copy_buffer_rect (OpenCL::Queue this, OpenCL::Buffer src, OpenCL::Buffer dst, size_t src_x, size_t src_y, size_t src_z, size_t dst_x, size_t dst_y, size_t dst_z, size_t width, size_t height, size_t depth, size_t src_row_pitch, size_t src_slice_pitch, size_t dst_row_pitch, size_t dst_slice_pitch, ...)
		1234	PPCODE:
		1235	cl_event ev = 0;
		1236	const size_t src_origin[3] = { src_x, src_y, src_z };
		1237	const size_t dst_origin[3] = { dst_x, dst_y, dst_z };
		1238	const size_t region[3] = { width, height, depth };
		1239	EVENT_LIST (16, items - 16);
		1240
		1241	NEED_SUCCESS (EnqueueCopyBufferRect, (this, src, dst, src_origin, dst_origin, region, src_row_pitch, src_slice_pitch, dst_row_pitch, dst_slice_pitch, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1242
		1243	if (ev)
		1244	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1245
		1246	void
		1247	enqueue_copy_buffer_to_image (OpenCL::Queue this, OpenCL::Buffer src, OpenCL::Image dst, size_t src_offset, size_t dst_x, size_t dst_y, size_t dst_z, size_t width, size_t height, size_t depth, ...)
		1248	PPCODE:
		1249	cl_event ev = 0;
		1250	const size_t dst_origin[3] = { dst_x, dst_y, dst_z };
		1251	const size_t region[3] = { width, height, depth };
		1252	EVENT_LIST (10, items - 10);
		1253
		1254	NEED_SUCCESS (EnqueueCopyBufferToImage, (this, src, dst, src_offset, dst_origin, region, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1255
		1256	if (ev)
		1257	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1258
		1259	void
		1260	enqueue_copy_image (OpenCL::Queue this, OpenCL::Image src, OpenCL::Image dst, size_t src_x, size_t src_y, size_t src_z, size_t dst_x, size_t dst_y, size_t dst_z, size_t width, size_t height, size_t depth, ...)
		1261	PPCODE:
		1262	cl_event ev = 0;
		1263	const size_t src_origin[3] = { src_x, src_y, src_z };
		1264	const size_t dst_origin[3] = { dst_x, dst_y, dst_z };
		1265	const size_t region[3] = { width, height, depth };
		1266	EVENT_LIST (12, items - 12);
		1267
		1268	NEED_SUCCESS (EnqueueCopyImage, (this, src, dst, src_origin, dst_origin, region, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1269
		1270	if (ev)
		1271	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1272
		1273	void
		1274	enqueue_copy_image_to_buffer (OpenCL::Queue this, OpenCL::Image src, OpenCL::Buffer dst, size_t src_x, size_t src_y, size_t src_z, size_t width, size_t height, size_t depth, size_t dst_offset, ...)
		1275	PPCODE:
		1276	cl_event ev = 0;
		1277	const size_t src_origin[3] = { src_x, src_y, src_z };
		1278	const size_t region[3] = { width, height, depth };
		1279	EVENT_LIST (10, items - 10);
		1280
		1281	NEED_SUCCESS (EnqueueCopyImageToBuffer, (this, src, dst, src_origin, region, dst_offset, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1282
		1283	if (ev)
		1284	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1285
		1286	void
		1287	enqueue_task (OpenCL::Queue this, OpenCL::Kernel kernel, ...)
		1288	PPCODE:
		1289	cl_event ev = 0;
		1290	EVENT_LIST (2, items - 2);
		1291
		1292	NEED_SUCCESS (EnqueueTask, (this, kernel, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1293
		1294	if (ev)
		1295	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
		1296
		1297	void
		1298	enqueue_nd_range_kernel (OpenCL::Queue this, OpenCL::Kernel kernel, SV *global_work_offset, SV *global_work_size, SV *local_work_size = &PL_sv_undef, ...)
		1299	PPCODE:
		1300	cl_event ev = 0;
		1301	size_t *gwo = 0, *gws, *lws = 0;
		1302	int gws_len;
		1303	size_t *lists;
		1304	int i;
		1305	EVENT_LIST (5, items - 5);
		1306
		1307	if (!SvROK (global_work_size) || SvTYPE (SvRV (global_work_size)) != SVt_PVAV)
		1308	croak ("clEnqueueNDRangeKernel: global_work_size must be an array reference");
		1309
		1310	gws_len = AvFILLp (SvRV (global_work_size)) + 1;
		1311
		1312	lists = tmpbuf (sizeof (size_t) * 3 * gws_len);
		1313
		1314	gws = lists + gws_len * 0;
		1315	for (i = 0; i < gws_len; ++i)
		1316	gws [i] = SvIV (AvARRAY (SvRV (global_work_size))[i]);
		1317
		1318	if (SvOK (global_work_offset))
		1319	{
		1320	if (!SvROK (global_work_offset) || SvTYPE (SvRV (global_work_offset)) != SVt_PVAV)
		1321	croak ("clEnqueueNDRangeKernel: global_work_offset must be undef or an array reference");
		1322
		1323	if (AvFILLp (SvRV (global_work_size)) + 1 != gws_len)
		1324	croak ("clEnqueueNDRangeKernel: global_work_offset must be undef or an array of same size as global_work_size");
		1325
		1326	gwo = lists + gws_len * 1;
		1327	for (i = 0; i < gws_len; ++i)
		1328	gwo [i] = SvIV (AvARRAY (SvRV (global_work_offset))[i]);
		1329	}
		1330
		1331	if (SvOK (local_work_size))
		1332	{
		1333	if (SvOK (local_work_size) && !SvROK (local_work_size) || SvTYPE (SvRV (local_work_size)) != SVt_PVAV)
		1334	croak ("clEnqueueNDRangeKernel: global_work_size must be undef or an array reference");
		1335
		1336	if (AvFILLp (SvRV (local_work_size)) + 1 != gws_len)
		1337	croak ("clEnqueueNDRangeKernel: local_work_local must be undef or an array of same size as global_work_size");
		1338
		1339	lws = lists + gws_len * 2;
		1340	for (i = 0; i < gws_len; ++i)
		1341	lws [i] = SvIV (AvARRAY (SvRV (local_work_size))[i]);
		1342	}
		1343
		1344	NEED_SUCCESS (EnqueueNDRangeKernel, (this, kernel, gws_len, gwo, gws, lws, event_list_count, event_list_ptr, GIMME_V != G_VOID ? &ev : 0));
		1345
		1346	if (ev)
		1347	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
337		1348
338	void	1349	void
339	enqueue_marker (OpenCL::Queue this)	1350	enqueue_marker (OpenCL::Queue this)
340	PPCODE:	1351	PPCODE:
341	{
342	cl_event ev;	1352	cl_event ev;
343	NEED_SUCCESS (EnqueueMarker, (this, &ev));	1353	NEED_SUCCESS (EnqueueMarker, (this, &ev));
344	XPUSH_NEW_OBJ ("OpenCL::Event", ev);	1354	XPUSH_NEW_OBJ ("OpenCL::Event", ev);
345	}
346		1355
347	void	1356	void
348	enqueue_wait_for_events (OpenCL::Queue this, ...)	1357	enqueue_wait_for_events (OpenCL::Queue this, ...)
349	CODE:	1358	CODE:
350	{
351	EVENT_LIST (1, items - 1);	1359	EVENT_LIST (1, items - 1);
352	NEED_SUCCESS (EnqueueWaitForEvents, (this, event_list_count, event_list_ptr));	1360	NEED_SUCCESS (EnqueueWaitForEvents, (this, event_list_count, event_list_ptr));
353	}
354		1361
355	void	1362	void
356	enqueue_barrier (OpenCL::Queue this)	1363	enqueue_barrier (OpenCL::Queue this)
357	CODE:	1364	CODE:
358	NEED_SUCCESS (EnqueueBarrier, (this));	1365	NEED_SUCCESS (EnqueueBarrier, (this));
359		1366
		1367	void
		1368	flush (OpenCL::Queue this)
		1369	CODE:
		1370	NEED_SUCCESS (Flush, (this));
		1371
		1372	void
		1373	finish (OpenCL::Queue this)
		1374	CODE:
		1375	NEED_SUCCESS (Finish, (this));
		1376
		1377	void
		1378	info (OpenCL::Queue this, cl_command_queue_info name)
		1379	PPCODE:
		1380	INFO (CommandQueue)
		1381
		1382	#BEGIN:command_queue
		1383
		1384	void
		1385	context (OpenCL::Queue this)
		1386	PPCODE:
		1387	cl_context value [1];
		1388	NEED_SUCCESS (GetCommandQueueInfo, (this, CL_QUEUE_CONTEXT, sizeof (value), value, 0));
		1389	EXTEND (SP, 1);
		1390	const int i = 0;
		1391	{
		1392	NEED_SUCCESS (RetainContext, (value [i]));
		1393	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		1394	}
		1395
		1396	void
		1397	device (OpenCL::Queue this)
		1398	PPCODE:
		1399	cl_device_id value [1];
		1400	NEED_SUCCESS (GetCommandQueueInfo, (this, CL_QUEUE_DEVICE, sizeof (value), value, 0));
		1401	EXTEND (SP, 1);
		1402	const int i = 0;
		1403	{
		1404	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Device", value [i]));
		1405	}
		1406
		1407	void
		1408	reference_count (OpenCL::Queue this)
		1409	PPCODE:
		1410	cl_uint value [1];
		1411	NEED_SUCCESS (GetCommandQueueInfo, (this, CL_QUEUE_REFERENCE_COUNT, sizeof (value), value, 0));
		1412	EXTEND (SP, 1);
		1413	const int i = 0;
		1414	PUSHs (sv_2mortal (newSVuv (value [i])));
		1415
		1416	void
		1417	properties (OpenCL::Queue this)
		1418	PPCODE:
		1419	cl_command_queue_properties value [1];
		1420	NEED_SUCCESS (GetCommandQueueInfo, (this, CL_QUEUE_PROPERTIES, sizeof (value), value, 0));
		1421	EXTEND (SP, 1);
		1422	const int i = 0;
		1423	PUSHs (sv_2mortal (newSViv (value [i])));
		1424
		1425	#END:command_queue
		1426
360	MODULE = OpenCL PACKAGE = OpenCL::Memory	1427	MODULE = OpenCL PACKAGE = OpenCL::Memory
361		1428
362	void	1429	void
363	DESTROY (OpenCL::Memory this)	1430	DESTROY (OpenCL::Memory this)
364	CODE:	1431	CODE:
…		…
367	void	1434	void
368	info (OpenCL::Memory this, cl_mem_info name)	1435	info (OpenCL::Memory this, cl_mem_info name)
369	PPCODE:	1436	PPCODE:
370	INFO (MemObject)	1437	INFO (MemObject)
371		1438
		1439	#BEGIN:mem
		1440
		1441	void
		1442	type (OpenCL::Memory this)
		1443	PPCODE:
		1444	cl_mem_object_type value [1];
		1445	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_TYPE, sizeof (value), value, 0));
		1446	EXTEND (SP, 1);
		1447	const int i = 0;
		1448	PUSHs (sv_2mortal (newSViv (value [i])));
		1449
		1450	void
		1451	flags (OpenCL::Memory this)
		1452	PPCODE:
		1453	cl_mem_flags value [1];
		1454	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_FLAGS, sizeof (value), value, 0));
		1455	EXTEND (SP, 1);
		1456	const int i = 0;
		1457	PUSHs (sv_2mortal (newSViv (value [i])));
		1458
		1459	void
		1460	size (OpenCL::Memory this)
		1461	PPCODE:
		1462	size_t value [1];
		1463	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_SIZE, sizeof (value), value, 0));
		1464	EXTEND (SP, 1);
		1465	const int i = 0;
		1466	PUSHs (sv_2mortal (newSVuv (value [i])));
		1467
		1468	void
		1469	host_ptr (OpenCL::Memory this)
		1470	PPCODE:
		1471	void * value [1];
		1472	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_HOST_PTR, sizeof (value), value, 0));
		1473	EXTEND (SP, 1);
		1474	const int i = 0;
		1475	PUSHs (sv_2mortal (newSVuv ((IV)(intptr_t)value [i])));
		1476
		1477	void
		1478	map_count (OpenCL::Memory this)
		1479	PPCODE:
		1480	cl_uint value [1];
		1481	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_MAP_COUNT, sizeof (value), value, 0));
		1482	EXTEND (SP, 1);
		1483	const int i = 0;
		1484	PUSHs (sv_2mortal (newSVuv (value [i])));
		1485
		1486	void
		1487	reference_count (OpenCL::Memory this)
		1488	PPCODE:
		1489	cl_uint value [1];
		1490	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_REFERENCE_COUNT, sizeof (value), value, 0));
		1491	EXTEND (SP, 1);
		1492	const int i = 0;
		1493	PUSHs (sv_2mortal (newSVuv (value [i])));
		1494
		1495	void
		1496	context (OpenCL::Memory this)
		1497	PPCODE:
		1498	cl_context value [1];
		1499	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_CONTEXT, sizeof (value), value, 0));
		1500	EXTEND (SP, 1);
		1501	const int i = 0;
		1502	{
		1503	NEED_SUCCESS (RetainContext, (value [i]));
		1504	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		1505	}
		1506
		1507	void
		1508	associated_memobject (OpenCL::Memory this)
		1509	PPCODE:
		1510	cl_mem value [1];
		1511	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_ASSOCIATED_MEMOBJECT, sizeof (value), value, 0));
		1512	EXTEND (SP, 1);
		1513	const int i = 0;
		1514	{
		1515	NEED_SUCCESS (RetainMemObject, (value [i]));
		1516	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Memory", value [i]));
		1517	}
		1518
		1519	void
		1520	offset (OpenCL::Memory this)
		1521	PPCODE:
		1522	size_t value [1];
		1523	NEED_SUCCESS (GetMemObjectInfo, (this, CL_MEM_OFFSET, sizeof (value), value, 0));
		1524	EXTEND (SP, 1);
		1525	const int i = 0;
		1526	PUSHs (sv_2mortal (newSVuv (value [i])));
		1527
		1528	#END:mem
		1529
		1530	MODULE = OpenCL PACKAGE = OpenCL::Image
		1531
		1532	void
		1533	image_info (OpenCL::Image this, cl_image_info name)
		1534	PPCODE:
		1535	INFO (Image)
		1536
		1537	#BEGIN:image
		1538
		1539	void
		1540	element_size (OpenCL::Image this)
		1541	PPCODE:
		1542	size_t value [1];
		1543	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_ELEMENT_SIZE, sizeof (value), value, 0));
		1544	EXTEND (SP, 1);
		1545	const int i = 0;
		1546	PUSHs (sv_2mortal (newSVuv (value [i])));
		1547
		1548	void
		1549	row_pitch (OpenCL::Image this)
		1550	PPCODE:
		1551	size_t value [1];
		1552	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_ROW_PITCH, sizeof (value), value, 0));
		1553	EXTEND (SP, 1);
		1554	const int i = 0;
		1555	PUSHs (sv_2mortal (newSVuv (value [i])));
		1556
		1557	void
		1558	slice_pitch (OpenCL::Image this)
		1559	PPCODE:
		1560	size_t value [1];
		1561	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_SLICE_PITCH, sizeof (value), value, 0));
		1562	EXTEND (SP, 1);
		1563	const int i = 0;
		1564	PUSHs (sv_2mortal (newSVuv (value [i])));
		1565
		1566	void
		1567	width (OpenCL::Image this)
		1568	PPCODE:
		1569	size_t value [1];
		1570	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_WIDTH, sizeof (value), value, 0));
		1571	EXTEND (SP, 1);
		1572	const int i = 0;
		1573	PUSHs (sv_2mortal (newSVuv (value [i])));
		1574
		1575	void
		1576	height (OpenCL::Image this)
		1577	PPCODE:
		1578	size_t value [1];
		1579	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_HEIGHT, sizeof (value), value, 0));
		1580	EXTEND (SP, 1);
		1581	const int i = 0;
		1582	PUSHs (sv_2mortal (newSVuv (value [i])));
		1583
		1584	void
		1585	depth (OpenCL::Image this)
		1586	PPCODE:
		1587	size_t value [1];
		1588	NEED_SUCCESS (GetImageInfo, (this, CL_IMAGE_DEPTH, sizeof (value), value, 0));
		1589	EXTEND (SP, 1);
		1590	const int i = 0;
		1591	PUSHs (sv_2mortal (newSVuv (value [i])));
		1592
		1593	#END:image
		1594
372	MODULE = OpenCL PACKAGE = OpenCL::Sampler	1595	MODULE = OpenCL PACKAGE = OpenCL::Sampler
373		1596
374	void	1597	void
375	DESTROY (OpenCL::Sampler this)	1598	DESTROY (OpenCL::Sampler this)
376	CODE:	1599	CODE:
…		…
379	void	1602	void
380	info (OpenCL::Sampler this, cl_sampler_info name)	1603	info (OpenCL::Sampler this, cl_sampler_info name)
381	PPCODE:	1604	PPCODE:
382	INFO (Sampler)	1605	INFO (Sampler)
383		1606
		1607	#BEGIN:sampler
		1608
		1609	void
		1610	reference_count (OpenCL::Sampler this)
		1611	PPCODE:
		1612	cl_uint value [1];
		1613	NEED_SUCCESS (GetSamplerInfo, (this, CL_SAMPLER_REFERENCE_COUNT, sizeof (value), value, 0));
		1614	EXTEND (SP, 1);
		1615	const int i = 0;
		1616	PUSHs (sv_2mortal (newSVuv (value [i])));
		1617
		1618	void
		1619	context (OpenCL::Sampler this)
		1620	PPCODE:
		1621	cl_context value [1];
		1622	NEED_SUCCESS (GetSamplerInfo, (this, CL_SAMPLER_CONTEXT, sizeof (value), value, 0));
		1623	EXTEND (SP, 1);
		1624	const int i = 0;
		1625	{
		1626	NEED_SUCCESS (RetainContext, (value [i]));
		1627	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		1628	}
		1629
		1630	void
		1631	normalized_coords (OpenCL::Sampler this)
		1632	PPCODE:
		1633	cl_addressing_mode value [1];
		1634	NEED_SUCCESS (GetSamplerInfo, (this, CL_SAMPLER_NORMALIZED_COORDS, sizeof (value), value, 0));
		1635	EXTEND (SP, 1);
		1636	const int i = 0;
		1637	PUSHs (sv_2mortal (newSViv (value [i])));
		1638
		1639	void
		1640	addressing_mode (OpenCL::Sampler this)
		1641	PPCODE:
		1642	cl_filter_mode value [1];
		1643	NEED_SUCCESS (GetSamplerInfo, (this, CL_SAMPLER_ADDRESSING_MODE, sizeof (value), value, 0));
		1644	EXTEND (SP, 1);
		1645	const int i = 0;
		1646	PUSHs (sv_2mortal (newSViv (value [i])));
		1647
		1648	void
		1649	filter_mode (OpenCL::Sampler this)
		1650	PPCODE:
		1651	cl_bool value [1];
		1652	NEED_SUCCESS (GetSamplerInfo, (this, CL_SAMPLER_FILTER_MODE, sizeof (value), value, 0));
		1653	EXTEND (SP, 1);
		1654	const int i = 0;
		1655	PUSHs (sv_2mortal (value [i] ? &PL_sv_yes : &PL_sv_no));
		1656
		1657	#END:sampler
		1658
384	MODULE = OpenCL PACKAGE = OpenCL::Program	1659	MODULE = OpenCL PACKAGE = OpenCL::Program
385		1660
386	void	1661	void
387	DESTROY (OpenCL::Program this)	1662	DESTROY (OpenCL::Program this)
388	CODE:	1663	CODE:
389	clReleaseProgram (this);	1664	clReleaseProgram (this);
390		1665
391	void	1666	void
392	info (OpenCL::Program this, cl_program_info name)
393	PPCODE:
394	INFO (Program)
395
396	void
397	build (OpenCL::Program this, OpenCL::Device device, SV *options = &PL_sv_undef)	1667	build (OpenCL::Program this, OpenCL::Device device, SV *options = &PL_sv_undef)
398	CODE:	1668	CODE:
399	NEED_SUCCESS (BuildProgram, (this, 1, &device, SvPVbyte_nolen (options), 0, 0));	1669	NEED_SUCCESS (BuildProgram, (this, 1, &device, SvPVbyte_nolen (options), 0, 0));
400		1670
401	void	1671	void
402	build_info (OpenCL::Program this, OpenCL::Device device, cl_program_build_info name)	1672	build_info (OpenCL::Program this, OpenCL::Device device, cl_program_build_info name)
403	PPCODE:	1673	PPCODE:
404	{
405	size_t size;	1674	size_t size;
406	SV *sv;
407
408	NEED_SUCCESS (GetProgramBuildInfo, (this, device, name, 0, 0, &size));	1675	NEED_SUCCESS (GetProgramBuildInfo, (this, device, name, 0, 0, &size));
409	sv = sv_2mortal (newSV (size));	1676	SV *sv = sv_2mortal (newSV (size));
410	SvUPGRADE (sv, SVt_PV);	1677	SvUPGRADE (sv, SVt_PV);
411	SvPOK_only (sv);	1678	SvPOK_only (sv);
412	SvCUR_set (sv, size);	1679	SvCUR_set (sv, size);
413	NEED_SUCCESS (GetProgramBuildInfo, (this, device, name, size, SvPVX (sv), 0));	1680	NEED_SUCCESS (GetProgramBuildInfo, (this, device, name, size, SvPVX (sv), 0));
414	XPUSHs (sv);	1681	XPUSHs (sv);
415	}	1682
		1683	#BEGIN:program_build
		1684
		1685	void
		1686	build_status (OpenCL::Program this, OpenCL::Device device)
		1687	PPCODE:
		1688	cl_build_status value [1];
		1689	NEED_SUCCESS (GetProgramBuildInfo, (this, device, CL_PROGRAM_BUILD_STATUS, sizeof (value), value, 0));
		1690	EXTEND (SP, 1);
		1691	const int i = 0;
		1692	PUSHs (sv_2mortal (newSViv (value [i])));
		1693
		1694	void
		1695	build_options (OpenCL::Program this, OpenCL::Device device)
		1696	PPCODE:
		1697	size_t size;
		1698	NEED_SUCCESS (GetProgramBuildInfo, (this, device, CL_PROGRAM_BUILD_OPTIONS, 0, 0, &size));
		1699	char *value = tmpbuf (size);
		1700	NEED_SUCCESS (GetProgramBuildInfo, (this, device, CL_PROGRAM_BUILD_OPTIONS, size, value, 0));
		1701	int i, n = 1;
		1702	EXTEND (SP, n);
		1703	for (i = 0; i < n; ++i)
		1704	PUSHs (sv_2mortal (newSVpv (value, 0)));
		1705
		1706	void
		1707	build_log (OpenCL::Program this, OpenCL::Device device)
		1708	PPCODE:
		1709	size_t size;
		1710	NEED_SUCCESS (GetProgramBuildInfo, (this, device, CL_PROGRAM_BUILD_LOG, 0, 0, &size));
		1711	char *value = tmpbuf (size);
		1712	NEED_SUCCESS (GetProgramBuildInfo, (this, device, CL_PROGRAM_BUILD_LOG, size, value, 0));
		1713	int i, n = 1;
		1714	EXTEND (SP, n);
		1715	for (i = 0; i < n; ++i)
		1716	PUSHs (sv_2mortal (newSVpv (value, 0)));
		1717
		1718	#END:program_build
416		1719
417	void	1720	void
418	kernel (OpenCL::Program program, SV *function)	1721	kernel (OpenCL::Program program, SV *function)
419	PPCODE:	1722	PPCODE:
420	{
421	cl_int res;
422	cl_kernel kernel = clCreateKernel (program, SvPVbyte_nolen (function), &res);	1723	NEED_SUCCESS_ARG (cl_kernel kernel, CreateKernel, (program, SvPVbyte_nolen (function), &res));
423
424	if (res)
425	FAIL (CreateKernel, res);
426
427	XPUSH_NEW_OBJ ("OpenCL::Kernel", kernel);	1724	XPUSH_NEW_OBJ ("OpenCL::Kernel", kernel);
428	}	1725
		1726	void
		1727	info (OpenCL::Program this, cl_program_info name)
		1728	PPCODE:
		1729	INFO (Program)
		1730
		1731	#BEGIN:program
		1732
		1733	void
		1734	reference_count (OpenCL::Program this)
		1735	PPCODE:
		1736	cl_uint value [1];
		1737	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_REFERENCE_COUNT, sizeof (value), value, 0));
		1738	EXTEND (SP, 1);
		1739	const int i = 0;
		1740	PUSHs (sv_2mortal (newSVuv (value [i])));
		1741
		1742	void
		1743	context (OpenCL::Program this)
		1744	PPCODE:
		1745	cl_context value [1];
		1746	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_CONTEXT, sizeof (value), value, 0));
		1747	EXTEND (SP, 1);
		1748	const int i = 0;
		1749	{
		1750	NEED_SUCCESS (RetainContext, (value [i]));
		1751	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		1752	}
		1753
		1754	void
		1755	num_devices (OpenCL::Program this)
		1756	PPCODE:
		1757	cl_uint value [1];
		1758	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_NUM_DEVICES, sizeof (value), value, 0));
		1759	EXTEND (SP, 1);
		1760	const int i = 0;
		1761	PUSHs (sv_2mortal (newSVuv (value [i])));
		1762
		1763	void
		1764	devices (OpenCL::Program this)
		1765	PPCODE:
		1766	size_t size;
		1767	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_DEVICES, 0, 0, &size));
		1768	cl_device_id *value = tmpbuf (size);
		1769	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_DEVICES, size, value, 0));
		1770	int i, n = size / sizeof (value [0]);
		1771	EXTEND (SP, n);
		1772	for (i = 0; i < n; ++i)
		1773	{
		1774	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Device", value [i]));
		1775	}
		1776
		1777	void
		1778	source (OpenCL::Program this)
		1779	PPCODE:
		1780	size_t size;
		1781	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_SOURCE, 0, 0, &size));
		1782	char *value = tmpbuf (size);
		1783	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_SOURCE, size, value, 0));
		1784	int i, n = 1;
		1785	EXTEND (SP, n);
		1786	for (i = 0; i < n; ++i)
		1787	PUSHs (sv_2mortal (newSVpv (value, 0)));
		1788
		1789	void
		1790	binary_sizes (OpenCL::Program this)
		1791	PPCODE:
		1792	size_t size;
		1793	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_BINARY_SIZES, 0, 0, &size));
		1794	size_t *value = tmpbuf (size);
		1795	NEED_SUCCESS (GetProgramInfo, (this, CL_PROGRAM_BINARY_SIZES, size, value, 0));
		1796	int i, n = size / sizeof (value [0]);
		1797	EXTEND (SP, n);
		1798	for (i = 0; i < n; ++i)
		1799	PUSHs (sv_2mortal (newSVuv (value [i])));
		1800
		1801	#END:program
429		1802
430	MODULE = OpenCL PACKAGE = OpenCL::Kernel	1803	MODULE = OpenCL PACKAGE = OpenCL::Kernel
431		1804
432	void	1805	void
433	DESTROY (OpenCL::Kernel this)	1806	DESTROY (OpenCL::Kernel this)
434	CODE:	1807	CODE:
435	clReleaseKernel (this);	1808	clReleaseKernel (this);
436		1809
437	void	1810	void
		1811	set_char (OpenCL::Kernel this, cl_uint idx, cl_char value)
		1812	CODE:
		1813	clSetKernelArg (this, idx, sizeof (value), &value);
		1814
		1815	void
		1816	set_uchar (OpenCL::Kernel this, cl_uint idx, cl_uchar value)
		1817	CODE:
		1818	clSetKernelArg (this, idx, sizeof (value), &value);
		1819
		1820	void
		1821	set_short (OpenCL::Kernel this, cl_uint idx, cl_short value)
		1822	CODE:
		1823	clSetKernelArg (this, idx, sizeof (value), &value);
		1824
		1825	void
		1826	set_ushort (OpenCL::Kernel this, cl_uint idx, cl_ushort value)
		1827	CODE:
		1828	clSetKernelArg (this, idx, sizeof (value), &value);
		1829
		1830	void
		1831	set_int (OpenCL::Kernel this, cl_uint idx, cl_int value)
		1832	CODE:
		1833	clSetKernelArg (this, idx, sizeof (value), &value);
		1834
		1835	void
		1836	set_uint (OpenCL::Kernel this, cl_uint idx, cl_uint value)
		1837	CODE:
		1838	clSetKernelArg (this, idx, sizeof (value), &value);
		1839
		1840	void
		1841	set_long (OpenCL::Kernel this, cl_uint idx, cl_long value)
		1842	CODE:
		1843	clSetKernelArg (this, idx, sizeof (value), &value);
		1844
		1845	void
		1846	set_ulong (OpenCL::Kernel this, cl_uint idx, cl_ulong value)
		1847	CODE:
		1848	clSetKernelArg (this, idx, sizeof (value), &value);
		1849
		1850	void
		1851	set_half (OpenCL::Kernel this, cl_uint idx, cl_half value)
		1852	CODE:
		1853	clSetKernelArg (this, idx, sizeof (value), &value);
		1854
		1855	void
		1856	set_float (OpenCL::Kernel this, cl_uint idx, cl_float value)
		1857	CODE:
		1858	clSetKernelArg (this, idx, sizeof (value), &value);
		1859
		1860	void
		1861	set_double (OpenCL::Kernel this, cl_uint idx, cl_double value)
		1862	CODE:
		1863	clSetKernelArg (this, idx, sizeof (value), &value);
		1864
		1865	void
		1866	set_memory (OpenCL::Kernel this, cl_uint idx, OpenCL::Memory_ornull value)
		1867	CODE:
		1868	clSetKernelArg (this, idx, sizeof (value), &value);
		1869
		1870	void
		1871	set_buffer (OpenCL::Kernel this, cl_uint idx, OpenCL::Buffer_ornull value)
		1872	CODE:
		1873	clSetKernelArg (this, idx, sizeof (value), &value);
		1874
		1875	void
		1876	set_image2d (OpenCL::Kernel this, cl_uint idx, OpenCL::Image2D_ornull value)
		1877	CODE:
		1878	clSetKernelArg (this, idx, sizeof (value), &value);
		1879
		1880	void
		1881	set_image3d (OpenCL::Kernel this, cl_uint idx, OpenCL::Image3D_ornull value)
		1882	CODE:
		1883	clSetKernelArg (this, idx, sizeof (value), &value);
		1884
		1885	void
		1886	set_sampler (OpenCL::Kernel this, cl_uint idx, OpenCL::Sampler value)
		1887	CODE:
		1888	clSetKernelArg (this, idx, sizeof (value), &value);
		1889
		1890	void
		1891	set_event (OpenCL::Kernel this, cl_uint idx, OpenCL::Event value)
		1892	CODE:
		1893	clSetKernelArg (this, idx, sizeof (value), &value);
		1894
		1895	void
438	info (OpenCL::Kernel this, cl_kernel_info name)	1896	info (OpenCL::Kernel this, cl_kernel_info name)
439	PPCODE:	1897	PPCODE:
440	INFO (Kernel)	1898	INFO (Kernel)
441		1899
		1900	#BEGIN:kernel
		1901
442	void	1902	void
443	set_bool (OpenCL::Kernel this, cl_uint idx, cl_bool value)	1903	function_name (OpenCL::Kernel this)
		1904	PPCODE:
		1905	size_t size;
		1906	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_FUNCTION_NAME, 0, 0, &size));
		1907	char *value = tmpbuf (size);
		1908	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_FUNCTION_NAME, size, value, 0));
		1909	int i, n = 1;
		1910	EXTEND (SP, n);
		1911	for (i = 0; i < n; ++i)
		1912	PUSHs (sv_2mortal (newSVpv (value, 0)));
		1913
		1914	void
		1915	num_args (OpenCL::Kernel this)
		1916	PPCODE:
		1917	cl_uint value [1];
		1918	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_NUM_ARGS, sizeof (value), value, 0));
		1919	EXTEND (SP, 1);
		1920	const int i = 0;
		1921	PUSHs (sv_2mortal (newSVuv (value [i])));
		1922
		1923	void
		1924	reference_count (OpenCL::Kernel this)
		1925	PPCODE:
		1926	cl_uint value [1];
		1927	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_REFERENCE_COUNT, sizeof (value), value, 0));
		1928	EXTEND (SP, 1);
		1929	const int i = 0;
		1930	PUSHs (sv_2mortal (newSVuv (value [i])));
		1931
		1932	void
		1933	context (OpenCL::Kernel this)
		1934	PPCODE:
		1935	cl_context value [1];
		1936	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_CONTEXT, sizeof (value), value, 0));
		1937	EXTEND (SP, 1);
		1938	const int i = 0;
		1939	{
		1940	NEED_SUCCESS (RetainContext, (value [i]));
		1941	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		1942	}
		1943
		1944	void
		1945	program (OpenCL::Kernel this)
		1946	PPCODE:
		1947	cl_program value [1];
		1948	NEED_SUCCESS (GetKernelInfo, (this, CL_KERNEL_PROGRAM, sizeof (value), value, 0));
		1949	EXTEND (SP, 1);
		1950	const int i = 0;
		1951	{
		1952	NEED_SUCCESS (RetainProgram, (value [i]));
		1953	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Program", value [i]));
		1954	}
		1955
		1956	#END:kernel
		1957
		1958	void
		1959	work_group_info (OpenCL::Kernel this, OpenCL::Device device, cl_kernel_work_group_info name)
444	CODE:	1960	PPCODE:
445	clKernelSetArg (this, idx, sizeof (value), &value);	1961	size_t size;
		1962	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, name, 0, 0, &size));
		1963	SV *sv = sv_2mortal (newSV (size));
		1964	SvUPGRADE (sv, SVt_PV);
		1965	SvPOK_only (sv);
		1966	SvCUR_set (sv, size);
		1967	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, name, size, SvPVX (sv), 0));
		1968	XPUSHs (sv);
		1969
		1970	#BEGIN:kernel_work_group
		1971
		1972	void
		1973	work_group_size (OpenCL::Kernel this, OpenCL::Device device)
		1974	PPCODE:
		1975	size_t value [1];
		1976	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_WORK_GROUP_SIZE, sizeof (value), value, 0));
		1977	EXTEND (SP, 1);
		1978	const int i = 0;
		1979	PUSHs (sv_2mortal (newSVuv (value [i])));
		1980
		1981	void
		1982	compile_work_group_size (OpenCL::Kernel this, OpenCL::Device device)
		1983	PPCODE:
		1984	size_t size;
		1985	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_COMPILE_WORK_GROUP_SIZE, 0, 0, &size));
		1986	size_t *value = tmpbuf (size);
		1987	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_COMPILE_WORK_GROUP_SIZE, size, value, 0));
		1988	int i, n = size / sizeof (value [0]);
		1989	EXTEND (SP, n);
		1990	for (i = 0; i < n; ++i)
		1991	PUSHs (sv_2mortal (newSVuv (value [i])));
		1992
		1993	void
		1994	local_mem_size (OpenCL::Kernel this, OpenCL::Device device)
		1995	PPCODE:
		1996	cl_ulong value [1];
		1997	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_LOCAL_MEM_SIZE, sizeof (value), value, 0));
		1998	EXTEND (SP, 1);
		1999	const int i = 0;
		2000	PUSHs (sv_2mortal (newSVuv (value [i])));
		2001
		2002	void
		2003	preferred_work_group_size_multiple (OpenCL::Kernel this, OpenCL::Device device)
		2004	PPCODE:
		2005	size_t value [1];
		2006	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE, sizeof (value), value, 0));
		2007	EXTEND (SP, 1);
		2008	const int i = 0;
		2009	PUSHs (sv_2mortal (newSVuv (value [i])));
		2010
		2011	void
		2012	private_mem_size (OpenCL::Kernel this, OpenCL::Device device)
		2013	PPCODE:
		2014	cl_ulong value [1];
		2015	NEED_SUCCESS (GetKernelWorkGroupInfo, (this, device, CL_KERNEL_PRIVATE_MEM_SIZE, sizeof (value), value, 0));
		2016	EXTEND (SP, 1);
		2017	const int i = 0;
		2018	PUSHs (sv_2mortal (newSVuv (value [i])));
		2019
		2020	#END:kernel_work_group
446		2021
447	MODULE = OpenCL PACKAGE = OpenCL::Event	2022	MODULE = OpenCL PACKAGE = OpenCL::Event
448		2023
449	void	2024	void
450	DESTROY (OpenCL::Event this)	2025	DESTROY (OpenCL::Event this)
451	CODE:	2026	CODE:
452	clReleaseEvent (this);	2027	clReleaseEvent (this);
453		2028
454	void	2029	void
		2030	wait (OpenCL::Event this)
		2031	CODE:
		2032	clWaitForEvents (1, &this);
		2033
		2034	void
455	info (OpenCL::Event this, cl_event_info name)	2035	info (OpenCL::Event this, cl_event_info name)
456	PPCODE:	2036	PPCODE:
457	INFO (Event)	2037	INFO (Event)
458		2038
		2039	#BEGIN:event
		2040
459	void	2041	void
		2042	command_queue (OpenCL::Event this)
		2043	PPCODE:
		2044	cl_command_queue value [1];
		2045	NEED_SUCCESS (GetEventInfo, (this, CL_EVENT_COMMAND_QUEUE, sizeof (value), value, 0));
		2046	EXTEND (SP, 1);
		2047	const int i = 0;
		2048	{
		2049	NEED_SUCCESS (RetainCommandQueue, (value [i]));
		2050	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Queue", value [i]));
		2051	}
		2052
		2053	void
		2054	command_type (OpenCL::Event this)
		2055	PPCODE:
		2056	cl_command_type value [1];
		2057	NEED_SUCCESS (GetEventInfo, (this, CL_EVENT_COMMAND_TYPE, sizeof (value), value, 0));
		2058	EXTEND (SP, 1);
		2059	const int i = 0;
		2060	PUSHs (sv_2mortal (newSVuv (value [i])));
		2061
		2062	void
		2063	reference_count (OpenCL::Event this)
		2064	PPCODE:
		2065	cl_uint value [1];
		2066	NEED_SUCCESS (GetEventInfo, (this, CL_EVENT_REFERENCE_COUNT, sizeof (value), value, 0));
		2067	EXTEND (SP, 1);
		2068	const int i = 0;
		2069	PUSHs (sv_2mortal (newSVuv (value [i])));
		2070
		2071	void
		2072	command_execution_status (OpenCL::Event this)
		2073	PPCODE:
		2074	cl_uint value [1];
		2075	NEED_SUCCESS (GetEventInfo, (this, CL_EVENT_COMMAND_EXECUTION_STATUS, sizeof (value), value, 0));
		2076	EXTEND (SP, 1);
		2077	const int i = 0;
		2078	PUSHs (sv_2mortal (newSVuv (value [i])));
		2079
		2080	void
460	wait (OpenCL::Event this)	2081	context (OpenCL::Event this)
		2082	PPCODE:
		2083	cl_context value [1];
		2084	NEED_SUCCESS (GetEventInfo, (this, CL_EVENT_CONTEXT, sizeof (value), value, 0));
		2085	EXTEND (SP, 1);
		2086	const int i = 0;
		2087	{
		2088	NEED_SUCCESS (RetainContext, (value [i]));
		2089	PUSHs (NEW_MORTAL_OBJ ("OpenCL::Context", value [i]));
		2090	}
		2091
		2092	#END:event
		2093
		2094	void
		2095	profiling_info (OpenCL::Event this, cl_profiling_info name)
461	CODE:	2096	PPCODE:
462	clWaitForEvents (1, &this);	2097	INFO (EventProfiling)
463		2098
		2099	#BEGIN:profiling
		2100
		2101	void
		2102	profiling_command_queued (OpenCL::Event this)
		2103	PPCODE:
		2104	cl_ulong value [1];
		2105	NEED_SUCCESS (GetEventProfilingInfo, (this, CL_PROFILING_COMMAND_QUEUED, sizeof (value), value, 0));
		2106	EXTEND (SP, 1);
		2107	const int i = 0;
		2108	PUSHs (sv_2mortal (newSVuv (value [i])));
		2109
		2110	void
		2111	profiling_command_submit (OpenCL::Event this)
		2112	PPCODE:
		2113	cl_ulong value [1];
		2114	NEED_SUCCESS (GetEventProfilingInfo, (this, CL_PROFILING_COMMAND_SUBMIT, sizeof (value), value, 0));
		2115	EXTEND (SP, 1);
		2116	const int i = 0;
		2117	PUSHs (sv_2mortal (newSVuv (value [i])));
		2118
		2119	void
		2120	profiling_command_start (OpenCL::Event this)
		2121	PPCODE:
		2122	cl_ulong value [1];
		2123	NEED_SUCCESS (GetEventProfilingInfo, (this, CL_PROFILING_COMMAND_START, sizeof (value), value, 0));
		2124	EXTEND (SP, 1);
		2125	const int i = 0;
		2126	PUSHs (sv_2mortal (newSVuv (value [i])));
		2127
		2128	void
		2129	profiling_command_end (OpenCL::Event this)
		2130	PPCODE:
		2131	cl_ulong value [1];
		2132	NEED_SUCCESS (GetEventProfilingInfo, (this, CL_PROFILING_COMMAND_END, sizeof (value), value, 0));
		2133	EXTEND (SP, 1);
		2134	const int i = 0;
		2135	PUSHs (sv_2mortal (newSVuv (value [i])));
		2136
		2137	#END:profiling
		2138
		2139	MODULE = OpenCL PACKAGE = OpenCL::UserEvent
		2140
		2141	void
		2142	set_status (OpenCL::UserEvent this, cl_int execution_status)
		2143	CODE:
		2144	clSetUserEventStatus (this, execution_status);
		2145

Diff Legend

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