Skip to content

Commit fbaafe1

Browse files
authored
Remove specific restrictions for custom devices (KhronosGroup#1388)
No guarantees are provided by custom devices at all. We should not call this out for specific queries. Change-Id: I7bf1730a94b72e1575f0703f42beb016b6a63d12 Signed-off-by: Kevin Petit <kevin.petit@arm.com>
1 parent 5babae6 commit fbaafe1

2 files changed

Lines changed: 14 additions & 27 deletions

File tree

api/embedded_profile.asciidoc

Lines changed: 5 additions & 10 deletions
Original file line numberDiff line numberDiff line change
@@ -216,8 +216,7 @@ Device Queries>> table.
216216
| {CL_DEVICE_MAX_PARAMETER_SIZE}
217217
| {size_t_TYPE}
218218
| Max size in bytes of all arguments that can be passed to a kernel.
219-
The minimum value is 256 bytes for devices that are not of type
220-
{CL_DEVICE_TYPE_CUSTOM}.
219+
The minimum value is 256 bytes.
221220

222221
A maximum of 255 arguments can be passed to a kernel.
223222
| {CL_DEVICE_SINGLE_FP_CONFIG}
@@ -248,24 +247,20 @@ Device Queries>> table.
248247

249248
[[embedded-profile-single-fp-config-requirements]]
250249
The mandated minimum floating-point capability is:
251-
{CL_FP_ROUND_TO_ZERO} or {CL_FP_ROUND_TO_NEAREST} for devices that are
252-
not of type {CL_DEVICE_TYPE_CUSTOM}.
250+
{CL_FP_ROUND_TO_ZERO} or {CL_FP_ROUND_TO_NEAREST}.
253251
| {CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE}
254252
| {cl_ulong_TYPE}
255253
| Max size in bytes of a constant buffer allocation.
256-
The minimum value is 1 KB for devices that are not of type
257-
{CL_DEVICE_TYPE_CUSTOM}.
254+
The minimum value is 1 KB.
258255
| {CL_DEVICE_MAX_CONSTANT_ARGS}
259256
| {cl_uint_TYPE}
260257
| Max number of arguments declared with the `+__constant+` qualifier
261258
in a kernel.
262-
The minimum value is 4 for devices that are not of type
263-
{CL_DEVICE_TYPE_CUSTOM}.
259+
The minimum value is 4.
264260
| {CL_DEVICE_LOCAL_MEM_SIZE}
265261
| {cl_ulong_TYPE}
266262
| Size of local memory arena in bytes.
267-
The minimum value is 1 KB for devices that are not of type
268-
{CL_DEVICE_TYPE_CUSTOM}.
263+
The minimum value is 1 KB.
269264
| {CL_DEVICE_COMPILER_AVAILABLE}
270265
| {cl_bool_TYPE}
271266
| Is {CL_FALSE} if the implementation does not have a compiler available

api/opencl_platform_layer.asciidoc

Lines changed: 9 additions & 17 deletions
Original file line numberDiff line numberDiff line change
@@ -552,8 +552,7 @@ include::{generated}/api/version-notes/CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS.asciid
552552
| Maximum dimensions that specify the global and local work-item IDs
553553
used by the data parallel execution model. (Refer to
554554
{clEnqueueNDRangeKernel}).
555-
The minimum value is 3 for devices that are not of type
556-
{CL_DEVICE_TYPE_CUSTOM}.
555+
The minimum value is 3.
557556
| {CL_DEVICE_MAX_WORK_ITEM_SIZES_anchor}
558557

559558
include::{generated}/api/version-notes/CL_DEVICE_MAX_WORK_ITEM_SIZES.asciidoc[]
@@ -564,8 +563,7 @@ include::{generated}/api/version-notes/CL_DEVICE_MAX_WORK_ITEM_SIZES.asciidoc[]
564563
Returns _n_ {size_t_TYPE} entries, where _n_ is the value returned by the
565564
query for {CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS}.
566565

567-
The minimum value is (1, 1, 1) for devices that are not of type
568-
{CL_DEVICE_TYPE_CUSTOM}.
566+
The minimum value is (1, 1, 1).
569567
| {CL_DEVICE_MAX_WORK_GROUP_SIZE_anchor}
570568

571569
include::{generated}/api/version-notes/CL_DEVICE_MAX_WORK_GROUP_SIZE.asciidoc[]
@@ -650,8 +648,7 @@ include::{generated}/api/version-notes/CL_DEVICE_MAX_MEM_ALLOC_SIZE.asciidoc[]
650648
| {cl_ulong_TYPE}
651649
| Max size of memory object allocation in bytes.
652650
The minimum value is max(min(1024 {times} 1024 {times} 1024, 1/4^th^
653-
of {CL_DEVICE_GLOBAL_MEM_SIZE}), 32 {times} 1024 {times} 1024) for
654-
devices that are not of type {CL_DEVICE_TYPE_CUSTOM}.
651+
of {CL_DEVICE_GLOBAL_MEM_SIZE}), 32 {times} 1024 {times} 1024).
655652
| {CL_DEVICE_IMAGE_SUPPORT_anchor}
656653

657654
include::{generated}/api/version-notes/CL_DEVICE_IMAGE_SUPPORT.asciidoc[]
@@ -916,8 +913,7 @@ include::{generated}/api/version-notes/CL_DEVICE_MAX_PARAMETER_SIZE.asciidoc[]
916913
| {size_t_TYPE}
917914
| Max size in bytes of all arguments that can be passed to a kernel.
918915

919-
The minimum value is 1024 for devices that are not of type
920-
{CL_DEVICE_TYPE_CUSTOM}.
916+
The minimum value is 1024.
921917
For this minimum value, only a maximum of 128 arguments can be
922918
passed to a kernel.
923919
For all other values, a maximum of 255 arguments can be passed
@@ -929,8 +925,7 @@ include::{generated}/api/version-notes/CL_DEVICE_MEM_BASE_ADDR_ALIGN.asciidoc[]
929925
| Alignment requirement (in bits) for sub-buffer offsets.
930926
The minimum value is the size (in bits) of the largest OpenCL
931927
built-in data type supported by the device (long16 in FULL profile,
932-
long16 or int16 in EMBEDDED profile) for devices that are not of
933-
type {CL_DEVICE_TYPE_CUSTOM}.
928+
long16 or int16 in EMBEDDED profile).
934929
| {CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE_anchor}
935930

936931
include::{generated}/api/version-notes/CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE.asciidoc[]
@@ -960,7 +955,7 @@ include::{generated}/api/version-notes/CL_DEVICE_SINGLE_FP_CONFIG.asciidoc[]
960955
addition, subtraction, multiplication) are implemented in software
961956

962957
For the full profile, the mandated minimum floating-point capability
963-
for devices that are not of type {CL_DEVICE_TYPE_CUSTOM} is:
958+
is:
964959

965960
{CL_FP_ROUND_TO_NEAREST} \| +
966961
{CL_FP_INF_NAN}.
@@ -1037,16 +1032,14 @@ include::{generated}/api/version-notes/CL_DEVICE_GLOBAL_MEM_SIZE.asciidoc[]
10371032
include::{generated}/api/version-notes/CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE.asciidoc[]
10381033
| {cl_ulong_TYPE}
10391034
| Max size in bytes of a constant buffer allocation.
1040-
The minimum value is 64 KB for devices that are not of type
1041-
{CL_DEVICE_TYPE_CUSTOM}.
1035+
The minimum value is 64 KB.
10421036
| {CL_DEVICE_MAX_CONSTANT_ARGS_anchor}
10431037

10441038
include::{generated}/api/version-notes/CL_DEVICE_MAX_CONSTANT_ARGS.asciidoc[]
10451039
| {cl_uint_TYPE}
10461040
| Max number of arguments declared with the `+__constant+` qualifier
10471041
in a kernel.
1048-
The minimum value is 8 for devices that are not of type
1049-
{CL_DEVICE_TYPE_CUSTOM}.
1042+
The minimum value is 8.
10501043
| {CL_DEVICE_MAX_GLOBAL_VARIABLE_SIZE_anchor}
10511044

10521045
include::{generated}/api/version-notes/CL_DEVICE_MAX_GLOBAL_VARIABLE_SIZE.asciidoc[]
@@ -1086,8 +1079,7 @@ include::{generated}/api/version-notes/CL_DEVICE_LOCAL_MEM_TYPE.asciidoc[]
10861079
include::{generated}/api/version-notes/CL_DEVICE_LOCAL_MEM_SIZE.asciidoc[]
10871080
| {cl_ulong_TYPE}
10881081
| Size of local memory region in bytes.
1089-
The minimum value is 32 KB for devices that are not of type
1090-
{CL_DEVICE_TYPE_CUSTOM}.
1082+
The minimum value is 32 KB.
10911083
| {CL_DEVICE_ERROR_CORRECTION_SUPPORT_anchor}
10921084

10931085
include::{generated}/api/version-notes/CL_DEVICE_ERROR_CORRECTION_SUPPORT.asciidoc[]

0 commit comments

Comments
 (0)