From 16d1dcc887d34e4823e9a25dd7d59d16552bce55 Mon Sep 17 00:00:00 2001 From: Sergey Kanaev Date: Thu, 10 Dec 2020 13:56:57 +0300 Subject: [PATCH 01/10] [SYCL] December'20 Release Notes Signed-off-by: Sergey Kanaev --- sycl/ReleaseNotes.md | 94 ++++++++++++++++++++++++++++++++++++++++++++ 1 file changed, 94 insertions(+) diff --git a/sycl/ReleaseNotes.md b/sycl/ReleaseNotes.md index cfe5a9504bb2b..f37f02afc35cb 100644 --- a/sycl/ReleaseNotes.md +++ b/sycl/ReleaseNotes.md @@ -1,3 +1,97 @@ +# December'20 release notes + +Release notes for commit range 5d7e0925..7c80f4491b31 + +## New features + +## Improvements +### SYCL Compiler + - Remove wrapping of buffer objects into images which caused problems like + incorrect work of scatter/gather of 1- and 2-byte values [d2d20d6c4556] +### SYCL Library + - Eliminate performance overhead on devies without host unified memory support + [a4f092417ef9] + - Implement dynamic batch suze adjusting when using Level-Zero plugin + [c70b0477aa8a, cf0d0538d162] + - Optimize `discard_write` access mode for host accessor [6733c8b0efde] + - Add support for composite specialization constants [c62860fd6b86] + - Enhance PI tracing with printing output arguments [19f5ad67f30a] +### Documentation + - Add information on AOT to GetStartedGuide [71942fbb3655] + - Add notice on alignemnt checks in ABI policy [4326b9563575] + - Updated design of specialization contants on using of POD types + [81963d1ec055] + - Document linked allocation commands [929a764a5ec4] + +## Bug fixes +### SYCL Compiler +### SYCL Library + - Add missing interoperability API to construct SYCL classes with Level-Zero + handles [10b4e8a6fc19] + - Fix several builtins implementation for host device + [8b82c671ab12, 786708914fd4] + - Fix possible hang upon application finish if streams were used [bd5893ae01b1] + - Fix build issue on Windows [c6b9973cceba] + - Fix failure when employing interoperability host task on queue constructed + with reused context [9cff6c9b6127] + - Fix build warnings of "instantiation after specialization" + [56b9a1dfb92f, eadce94f8ad0] + - Support passing of stream by value to kernel function without loss of + output information [8d37cbacc9b8] + - Fix handling of big and/or non-uniform work-groups in reduction kernels. The + solution may change when reduction kernels precompilation/query approach is + implemented [78e2599bc499] + - Fix memory leak in event pool in Level Zero plugin [68fc7808a50e] + - Fixed issue with finalizing context of Level Zero plugin [6cfa921856f5] +### Documentation + - Updated source checkout instruction for Windows in GetStartedGuide + [9cde15210d70] + +## API/ABI breakages + +## Known issues + - GlobalWorkOffset is not supported by Level Zero backend [6f9e9a76] + - The code with function pointer is hanging on Level Zero [d384295e] + - If an application uses `std::*` math function in the kernel code the + `-fsycl-device-lib=libm-fp64` option should be passed to the compiler. + - User-defined functions with the same name and signature (exact match of + arguments, return type doesn't matter) as of an OpenCL C built-in + function, can lead to Undefined Behavior. + - A DPC++ system that has FPGAs installed does not support multi-process + execution. Creating a context opens the device associated with the context + and places a lock on it for that process. No other process may use that + device. Some queries about the device through device.get_info<>() also + open up the device and lock it to that process since the runtime needs + to query the actual device to obtain that information. + - On Windows, DPC++ compiler enforces using dynamic C++ runtime for + application linked with SYCL library by: + - linking with msvcrt[d].dll when `-fsycl` switch is used; + - emitting an error on attempts to compile a program with static C++ RT + using `-fsycl` and `/MT` or `/MTd`. + That protects you from complicated runtime errors caused by C++ objects + crossing sycl[d].dll boundary and not always handled properly by different + versions of C++ RT used on app and sycl[d].dll sides. + - The format of the object files produced by the compiler can change between + versions. The workaround is to rebuild the application. + - The SYCL library doesn't guarantee stable API/ABI, so applications compiled + with older version of the SYCL library may not work with new one. + The workaround is to rebuild the application. + [ABI policy guide](doc/ABIPolicyGuide.md) + - Using `cl::sycl::program` API to refer to a kernel defined in another + translation unit leads to undefined behavior + - Linkage errors with the following message: + `error LNK2005: "bool const std::_Is_integral" (??$_Is_integral@_N@std@@3_NB) already defined` + can happen when a SYCL application is built using MS Visual Studio 2019 + version below 16.3.0 and user specifies `-std=c++14` or `/std:c++14`. + - Employing read sampler for image accessor may result in sporadic issues with + Level Zero plugin/backend [2c50c03] + - Printing internal defines isn't supported on Windows [50628db] + - Group algorithms for MUL/AND/OR/XOR cannot be enabled for group scope due to + SPIR-V limitations, and are not enabled for sub-group scope yet as the + SPIR-V version isn't automatically raised from 1.1 to 1.3 [96da39e] + - We cannot run Dead Argument Elimination for ESIMD since the pointers to SPIR + kernel functions are saved in `!genx.kernels metadata` [cf10351] + # November'20 release notes Release notes for commit range c9d50752..5d7e0925 From d65801df4061a04e9108b45b96480dc4a23321a5 Mon Sep 17 00:00:00 2001 From: Sergey Kanaev Date: Tue, 15 Dec 2020 14:23:04 +0300 Subject: [PATCH 02/10] [SYCL] Augment release notes Signed-off-by: Sergey Kanaev --- sycl/ReleaseNotes.md | 21 +++++++++++++++++++-- 1 file changed, 19 insertions(+), 2 deletions(-) diff --git a/sycl/ReleaseNotes.md b/sycl/ReleaseNotes.md index f37f02afc35cb..8ff8001d9cd80 100644 --- a/sycl/ReleaseNotes.md +++ b/sycl/ReleaseNotes.md @@ -1,13 +1,25 @@ # December'20 release notes -Release notes for commit range 5d7e0925..7c80f4491b31 +Release notes for commit range 5d7e0925..9d0e3525ba04 ## New features +### SYCL Compiler + - Allow for multiple build options for opencl-aot [5e5703f58449] +### SYCL Library +### Documentation + - Proposal for new device descriptors was added [1ad813ba133e] ## Improvements ### SYCL Compiler - Remove wrapping of buffer objects into images which caused problems like incorrect work of scatter/gather of 1- and 2-byte values [d2d20d6c4556] + - Rename FPGA kernel attribute `[[intel::stall_enable]]` to + `[[intel::use_stall_enable_clusters]]` [dab9debebe70] + - Add template parameter support for `[[intel::max_global_work_dim]]` + attribute [bd8fcc7dee34] + - Remove partial-link path when dealing with fat static archives [f1aa7f4d8b79] + - Remove unused device library function definitions from linked program + [e9423ffdec92] ### SYCL Library - Eliminate performance overhead on devies without host unified memory support [a4f092417ef9] @@ -16,15 +28,20 @@ Release notes for commit range 5d7e0925..7c80f4491b31 - Optimize `discard_write` access mode for host accessor [6733c8b0efde] - Add support for composite specialization constants [c62860fd6b86] - Enhance PI tracing with printing output arguments [19f5ad67f30a] + - Introduce `pi_map_flags` in lieu of `cl_map_flags` [f0e7606a6198] ### Documentation - Add information on AOT to GetStartedGuide [71942fbb3655] - Add notice on alignemnt checks in ABI policy [4326b9563575] - Updated design of specialization contants on using of POD types [81963d1ec055] - Document linked allocation commands [929a764a5ec4] + - Improve ESIMD documentation rendering [079597d28f1f] ## Bug fixes ### SYCL Compiler + - Do not customize optimizations for non-SPIR targets [cb069fed6712] + - Fix address space assertion with templates [8905a8cec9a9] + - Don't dump IR and dot files by default in the LowerWGScope [9d0e3525ba04] ### SYCL Library - Add missing interoperability API to construct SYCL classes with Level-Zero handles [10b4e8a6fc19] @@ -34,7 +51,7 @@ Release notes for commit range 5d7e0925..7c80f4491b31 - Fix build issue on Windows [c6b9973cceba] - Fix failure when employing interoperability host task on queue constructed with reused context [9cff6c9b6127] - - Fix build warnings of "instantiation after specialization" + - Fix "instantiation after specialization" warnings [56b9a1dfb92f, eadce94f8ad0] - Support passing of stream by value to kernel function without loss of output information [8d37cbacc9b8] From 2046c58ff83afb9e74ec7ad7ab07fb1d73f677ad Mon Sep 17 00:00:00 2001 From: Sergey Kanaev Date: Tue, 15 Dec 2020 14:26:22 +0300 Subject: [PATCH 03/10] [SYCL] Fix typos Signed-off-by: Sergey Kanaev --- sycl/ReleaseNotes.md | 8 ++++---- 1 file changed, 4 insertions(+), 4 deletions(-) diff --git a/sycl/ReleaseNotes.md b/sycl/ReleaseNotes.md index 8ff8001d9cd80..bf90150b89ebb 100644 --- a/sycl/ReleaseNotes.md +++ b/sycl/ReleaseNotes.md @@ -21,9 +21,9 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 - Remove unused device library function definitions from linked program [e9423ffdec92] ### SYCL Library - - Eliminate performance overhead on devies without host unified memory support + - Eliminate performance overhead on devices without host unified memory support [a4f092417ef9] - - Implement dynamic batch suze adjusting when using Level-Zero plugin + - Implement dynamic batch size adjusting when using Level-Zero plugin [c70b0477aa8a, cf0d0538d162] - Optimize `discard_write` access mode for host accessor [6733c8b0efde] - Add support for composite specialization constants [c62860fd6b86] @@ -53,8 +53,8 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 with reused context [9cff6c9b6127] - Fix "instantiation after specialization" warnings [56b9a1dfb92f, eadce94f8ad0] - - Support passing of stream by value to kernel function without loss of - output information [8d37cbacc9b8] + - Support copying of stream by value within a kernel without loss of output + information [8d37cbacc9b8] - Fix handling of big and/or non-uniform work-groups in reduction kernels. The solution may change when reduction kernels precompilation/query approach is implemented [78e2599bc499] From 051206893f51c19db0ee8202508626ccdabbede7 Mon Sep 17 00:00:00 2001 From: Sergey Kanaev Date: Tue, 15 Dec 2020 17:14:08 +0300 Subject: [PATCH 04/10] [SYCL] Address review comments Signed-off-by: Sergey Kanaev --- sycl/ReleaseNotes.md | 7 +------ 1 file changed, 1 insertion(+), 6 deletions(-) diff --git a/sycl/ReleaseNotes.md b/sycl/ReleaseNotes.md index bf90150b89ebb..174127c72490d 100644 --- a/sycl/ReleaseNotes.md +++ b/sycl/ReleaseNotes.md @@ -20,6 +20,7 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 - Remove partial-link path when dealing with fat static archives [f1aa7f4d8b79] - Remove unused device library function definitions from linked program [e9423ffdec92] + - Don't dump IR and dot files by default in the LowerWGScope [9d0e3525ba04] ### SYCL Library - Eliminate performance overhead on devices without host unified memory support [a4f092417ef9] @@ -41,14 +42,12 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 ### SYCL Compiler - Do not customize optimizations for non-SPIR targets [cb069fed6712] - Fix address space assertion with templates [8905a8cec9a9] - - Don't dump IR and dot files by default in the LowerWGScope [9d0e3525ba04] ### SYCL Library - Add missing interoperability API to construct SYCL classes with Level-Zero handles [10b4e8a6fc19] - Fix several builtins implementation for host device [8b82c671ab12, 786708914fd4] - Fix possible hang upon application finish if streams were used [bd5893ae01b1] - - Fix build issue on Windows [c6b9973cceba] - Fix failure when employing interoperability host task on queue constructed with reused context [9cff6c9b6127] - Fix "instantiation after specialization" warnings @@ -90,10 +89,6 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 versions of C++ RT used on app and sycl[d].dll sides. - The format of the object files produced by the compiler can change between versions. The workaround is to rebuild the application. - - The SYCL library doesn't guarantee stable API/ABI, so applications compiled - with older version of the SYCL library may not work with new one. - The workaround is to rebuild the application. - [ABI policy guide](doc/ABIPolicyGuide.md) - Using `cl::sycl::program` API to refer to a kernel defined in another translation unit leads to undefined behavior - Linkage errors with the following message: From c69fbe22a7f1a80e2032a5e7a9ad42d6aecc4a34 Mon Sep 17 00:00:00 2001 From: Sergey Kanaev Date: Fri, 18 Dec 2020 05:56:54 -0800 Subject: [PATCH 05/10] [SYCL] Augment release notes Signed-off-by: Sergey Kanaev --- sycl/ReleaseNotes.md | 16 ++++++++++++---- 1 file changed, 12 insertions(+), 4 deletions(-) diff --git a/sycl/ReleaseNotes.md b/sycl/ReleaseNotes.md index 174127c72490d..cb0b85b2557d0 100644 --- a/sycl/ReleaseNotes.md +++ b/sycl/ReleaseNotes.md @@ -1,6 +1,6 @@ # December'20 release notes -Release notes for commit range 5d7e0925..9d0e3525ba04 +Release notes for commit range 5d7e0925..d4251e3c55e7 ## New features ### SYCL Compiler @@ -15,19 +15,23 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 incorrect work of scatter/gather of 1- and 2-byte values [d2d20d6c4556] - Rename FPGA kernel attribute `[[intel::stall_enable]]` to `[[intel::use_stall_enable_clusters]]` [dab9debebe70] - - Add template parameter support for `[[intel::max_global_work_dim]]` - attribute [bd8fcc7dee34] + - Add template parameter support for `[[intel::max_global_work_dim]]` and + `[[intel::no_global_work_offset]]` attributes [bd8fcc7dee34, a5fde5a924ac] - Remove partial-link path when dealing with fat static archives [f1aa7f4d8b79] - Remove unused device library function definitions from linked program [e9423ffdec92] - Don't dump IR and dot files by default in the LowerWGScope [9d0e3525ba04] + - Support LLVM FP intrinsics in llvm-spirv and in frontend [a5065ab85101] + - Improve group size selection by adjusting parallel-for global range size + [74a68b7da4e7] ### SYCL Library - Eliminate performance overhead on devices without host unified memory support [a4f092417ef9] - Implement dynamic batch size adjusting when using Level-Zero plugin [c70b0477aa8a, cf0d0538d162] - Optimize `discard_write` access mode for host accessor [6733c8b0efde] - - Add support for composite specialization constants [c62860fd6b86] + - Add support for composite specialization constants + [c62860fd6b86, d4251e3c55e7] - Enhance PI tracing with printing output arguments [19f5ad67f30a] - Introduce `pi_map_flags` in lieu of `cl_map_flags` [f0e7606a6198] ### Documentation @@ -42,6 +46,9 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 ### SYCL Compiler - Do not customize optimizations for non-SPIR targets [cb069fed6712] - Fix address space assertion with templates [8905a8cec9a9] + - Fixed support of specialization constant types declared in namespaces + [f64f835b4313] + - Link libm FP6 device library by default [ac93d6fe3d9d] ### SYCL Library - Add missing interoperability API to construct SYCL classes with Level-Zero handles [10b4e8a6fc19] @@ -59,6 +66,7 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 implemented [78e2599bc499] - Fix memory leak in event pool in Level Zero plugin [68fc7808a50e] - Fixed issue with finalizing context of Level Zero plugin [6cfa921856f5] + - Fix backend selection for `SYCL_DEVICE_FILTER=*` [c54da157f5d5] ### Documentation - Updated source checkout instruction for Windows in GetStartedGuide [9cde15210d70] From 5f645a4494ee9908dae33dce481c8ee5a9ad1d9c Mon Sep 17 00:00:00 2001 From: Sergey Kanaev Date: Tue, 22 Dec 2020 16:50:13 +0300 Subject: [PATCH 06/10] [SYCL] Augment notes Signed-off-by: Sergey Kanaev --- sycl/ReleaseNotes.md | 21 +++++++++++++++++++-- 1 file changed, 19 insertions(+), 2 deletions(-) diff --git a/sycl/ReleaseNotes.md b/sycl/ReleaseNotes.md index 174127c72490d..4b15f6a8c1292 100644 --- a/sycl/ReleaseNotes.md +++ b/sycl/ReleaseNotes.md @@ -1,6 +1,6 @@ # December'20 release notes -Release notes for commit range 5d7e0925..9d0e3525ba04 +Release notes for commit range 5d7e0925..eb89f5eaab37 ## New features ### SYCL Compiler @@ -21,15 +21,25 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 - Remove unused device library function definitions from linked program [e9423ffdec92] - Don't dump IR and dot files by default in the LowerWGScope [9d0e3525ba04] + - Link libm-fp64 device library by default [ac93d6fe3d9d] + - Support LLVM floating-point intrinsics in llvm-spirv and frontend + [a5065ab85101] + - Add template parameter support for `[[intel::no_global_work_offset()]]` + attribute [a5fde5a924ac] + - Improve group size selection by adjusting `parallel_for` execution range + global size [74a68b7da4e7] ### SYCL Library - Eliminate performance overhead on devices without host unified memory support [a4f092417ef9] - Implement dynamic batch size adjusting when using Level-Zero plugin [c70b0477aa8a, cf0d0538d162] - Optimize `discard_write` access mode for host accessor [6733c8b0efde] - - Add support for composite specialization constants [c62860fd6b86] + - Add support for composite specialization constants + [c62860fd6b86, d4251e3c55e7] - Enhance PI tracing with printing output arguments [19f5ad67f30a] - Introduce `pi_map_flags` in lieu of `cl_map_flags` [f0e7606a6198] + - Implement robust error nadling in LevelZero plugin [65c719ddfc23] + - Add online compilation API interface [70ac47d23264] ### Documentation - Add information on AOT to GetStartedGuide [71942fbb3655] - Add notice on alignemnt checks in ABI policy [4326b9563575] @@ -37,11 +47,17 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 [81963d1ec055] - Document linked allocation commands [929a764a5ec4] - Improve ESIMD documentation rendering [079597d28f1f] + - Improved device library documentation [f24e2a9ce464] + - Add online compilation specification [e05a19c8d303] ## Bug fixes ### SYCL Compiler - Do not customize optimizations for non-SPIR targets [cb069fed6712] - Fix address space assertion with templates [8905a8cec9a9] + - Add support for specialization constants' typenames declared in namespaces + [f64f835b4313] + - Fix loosing OpenMP device binary when program uses both OpenMP and SYCL + offloading models [eb89f5eaab37] ### SYCL Library - Add missing interoperability API to construct SYCL classes with Level-Zero handles [10b4e8a6fc19] @@ -59,6 +75,7 @@ Release notes for commit range 5d7e0925..9d0e3525ba04 implemented [78e2599bc499] - Fix memory leak in event pool in Level Zero plugin [68fc7808a50e] - Fixed issue with finalizing context of Level Zero plugin [6cfa921856f5] + - Fix backend selection for `SYCL_DEVICE_FILTER=*` case [c54da157f5d5] ### Documentation - Updated source checkout instruction for Windows in GetStartedGuide [9cde15210d70] From f4c504843d25ba17b98259808cdfb294823cd05c Mon Sep 17 00:00:00 2001 From: Sergey Kanaev Date: Tue, 22 Dec 2020 16:58:44 +0300 Subject: [PATCH 07/10] [SYCL] Augment notes Signed-off-by: Sergey Kanaev --- sycl/ReleaseNotes.md | 7 +++++-- 1 file changed, 5 insertions(+), 2 deletions(-) diff --git a/sycl/ReleaseNotes.md b/sycl/ReleaseNotes.md index 4b15f6a8c1292..54cc2a0b3abf0 100644 --- a/sycl/ReleaseNotes.md +++ b/sycl/ReleaseNotes.md @@ -1,6 +1,6 @@ # December'20 release notes -Release notes for commit range 5d7e0925..eb89f5eaab37 +Release notes for commit range 5d7e0925..50b81c3cd6e9 ## New features ### SYCL Compiler @@ -28,6 +28,8 @@ Release notes for commit range 5d7e0925..eb89f5eaab37 attribute [a5fde5a924ac] - Improve group size selection by adjusting `parallel_for` execution range global size [74a68b7da4e7] + - Add clang support for FPGA loop fusion function attributes [23926b0645ad] + - Reword some compiler diagnostics [50b81c3cd6e9] ### SYCL Library - Eliminate performance overhead on devices without host unified memory support [a4f092417ef9] @@ -35,7 +37,7 @@ Release notes for commit range 5d7e0925..eb89f5eaab37 [c70b0477aa8a, cf0d0538d162] - Optimize `discard_write` access mode for host accessor [6733c8b0efde] - Add support for composite specialization constants - [c62860fd6b86, d4251e3c55e7] + [c62860fd6b86, d4251e3c55e7, 3ec4594a5a06] - Enhance PI tracing with printing output arguments [19f5ad67f30a] - Introduce `pi_map_flags` in lieu of `cl_map_flags` [f0e7606a6198] - Implement robust error nadling in LevelZero plugin [65c719ddfc23] @@ -76,6 +78,7 @@ Release notes for commit range 5d7e0925..eb89f5eaab37 - Fix memory leak in event pool in Level Zero plugin [68fc7808a50e] - Fixed issue with finalizing context of Level Zero plugin [6cfa921856f5] - Fix backend selection for `SYCL_DEVICE_FILTER=*` case [c54da157f5d5] + - Restore AccessorImplHost layout [a08eeb475679] ### Documentation - Updated source checkout instruction for Windows in GetStartedGuide [9cde15210d70] From 15816c924c906f067285c3b2a03e20e1334c703a Mon Sep 17 00:00:00 2001 From: Sergey Kanaev Date: Wed, 23 Dec 2020 10:10:39 +0300 Subject: [PATCH 08/10] [SYCL] Augment notes Signed-off-by: Sergey Kanaev --- sycl/ReleaseNotes.md | 12 +++++++++--- 1 file changed, 9 insertions(+), 3 deletions(-) diff --git a/sycl/ReleaseNotes.md b/sycl/ReleaseNotes.md index 05b9bd43cd016..814c48928ea36 100644 --- a/sycl/ReleaseNotes.md +++ b/sycl/ReleaseNotes.md @@ -1,6 +1,6 @@ # December'20 release notes -Release notes for commit range 5d7e0925..50b81c3cd6e9 +Release notes for commit range 5d7e0925..5eebd1e4bfce ## New features ### SYCL Compiler @@ -11,8 +11,9 @@ Release notes for commit range 5d7e0925..50b81c3cd6e9 ## Improvements ### SYCL Compiler - - Remove wrapping of buffer objects into images which caused problems like - incorrect work of scatter/gather of 1- and 2-byte values [d2d20d6c4556] + - (ESIMD only) Remove wrapping of buffer objects into images which caused + problems like incorrect work of scatter/gather of 1- and 2-byte values + [d2d20d6c4556] - Rename FPGA kernel attribute `[[intel::stall_enable]]` to `[[intel::use_stall_enable_clusters]]` [dab9debebe70] - Add template parameter support for `[[intel::max_global_work_dim]]` and @@ -41,6 +42,11 @@ Release notes for commit range 5d7e0925..50b81c3cd6e9 - Introduce `pi_map_flags` in lieu of `cl_map_flags` [f0e7606a6198] - Implement robust error nadling in LevelZero plugin [65c719ddfc23] - Add online compilation API interface [70ac47d23264] + - Add new device descriptors as SYCL extensions [51ac08c35294] + - Implement [`SYCL_INTEL_mem_channel_property`](doc/extensions/MemChannel/SYCL_INTEL_mem_channel_property.asciidoc) + extension [2f1f3167b7c6] + - Remove redundant dependencies for in-order queues [632722165db2] + - Add `marray` class as defined by SYCL 2020 provisional [5eebd1e4bfce] ### Documentation - Add information on AOT to GetStartedGuide [71942fbb3655] - Add notice on alignemnt checks in ABI policy [4326b9563575] From cab2a0e18f7ba5345d6c9b61b0baad3c95308c47 Mon Sep 17 00:00:00 2001 From: Sergey Kanaev Date: Wed, 23 Dec 2020 11:06:06 +0300 Subject: [PATCH 09/10] [SYCL] Slight reword and shuffle Signed-off-by: Sergey Kanaev --- sycl/ReleaseNotes.md | 20 +++++++++++--------- 1 file changed, 11 insertions(+), 9 deletions(-) diff --git a/sycl/ReleaseNotes.md b/sycl/ReleaseNotes.md index 814c48928ea36..f1a15a37624b3 100644 --- a/sycl/ReleaseNotes.md +++ b/sycl/ReleaseNotes.md @@ -6,8 +6,17 @@ Release notes for commit range 5d7e0925..5eebd1e4bfce ### SYCL Compiler - Allow for multiple build options for opencl-aot [5e5703f58449] ### SYCL Library + - Implement [`SYCL_INTEL_mem_channel_property`](doc/extensions/MemChannel/SYCL_INTEL_mem_channel_property.asciidoc) + extension [2f1f3167b7c6] + - Add `marray` class as defined by SYCL 2020 provisional [5eebd1e4bfce] + - Implement dynamic batch size adjusting when using Level-Zero plugin + [c70b0477aa8a, cf0d0538d162] + - Add online compilation API interface [70ac47d23264] ### Documentation - - Proposal for new device descriptors was added [1ad813ba133e] + - Proposal for [new device descriptors extension](doc/extensions/IntelGPU/IntelGPUDeviceInfo.md) + was added [1ad813ba133e] + - Added [online compilation extension](doc/extensions/OnlineCompilation/OnlineCompilation.asciidoc) + specification [e05a19c8d303] ## Improvements ### SYCL Compiler @@ -33,20 +42,14 @@ Release notes for commit range 5d7e0925..5eebd1e4bfce ### SYCL Library - Eliminate performance overhead on devices without host unified memory support [a4f092417ef9] - - Implement dynamic batch size adjusting when using Level-Zero plugin - [c70b0477aa8a, cf0d0538d162] - Optimize `discard_write` access mode for host accessor [6733c8b0efde] - Add support for composite specialization constants [c62860fd6b86, d4251e3c55e7, 3ec4594a5a06] - Enhance PI tracing with printing output arguments [19f5ad67f30a] - Introduce `pi_map_flags` in lieu of `cl_map_flags` [f0e7606a6198] - - Implement robust error nadling in LevelZero plugin [65c719ddfc23] - - Add online compilation API interface [70ac47d23264] + - Implement robust error handling in LevelZero plugin [65c719ddfc23] - Add new device descriptors as SYCL extensions [51ac08c35294] - - Implement [`SYCL_INTEL_mem_channel_property`](doc/extensions/MemChannel/SYCL_INTEL_mem_channel_property.asciidoc) - extension [2f1f3167b7c6] - Remove redundant dependencies for in-order queues [632722165db2] - - Add `marray` class as defined by SYCL 2020 provisional [5eebd1e4bfce] ### Documentation - Add information on AOT to GetStartedGuide [71942fbb3655] - Add notice on alignemnt checks in ABI policy [4326b9563575] @@ -55,7 +58,6 @@ Release notes for commit range 5d7e0925..5eebd1e4bfce - Document linked allocation commands [929a764a5ec4] - Improve ESIMD documentation rendering [079597d28f1f] - Improved device library documentation [f24e2a9ce464] - - Add online compilation specification [e05a19c8d303] ## Bug fixes ### SYCL Compiler From ee891fbd05501713fccd8ab65d5b0e104ed915c0 Mon Sep 17 00:00:00 2001 From: Sergey Kanaev Date: Wed, 23 Dec 2020 11:06:46 +0300 Subject: [PATCH 10/10] [SYCL] Remove one bullet of known issues Signed-off-by: Sergey Kanaev --- sycl/ReleaseNotes.md | 2 -- 1 file changed, 2 deletions(-) diff --git a/sycl/ReleaseNotes.md b/sycl/ReleaseNotes.md index f1a15a37624b3..8a320864850b5 100644 --- a/sycl/ReleaseNotes.md +++ b/sycl/ReleaseNotes.md @@ -96,8 +96,6 @@ Release notes for commit range 5d7e0925..5eebd1e4bfce ## Known issues - GlobalWorkOffset is not supported by Level Zero backend [6f9e9a76] - The code with function pointer is hanging on Level Zero [d384295e] - - If an application uses `std::*` math function in the kernel code the - `-fsycl-device-lib=libm-fp64` option should be passed to the compiler. - User-defined functions with the same name and signature (exact match of arguments, return type doesn't matter) as of an OpenCL C built-in function, can lead to Undefined Behavior.