Filip Hazubski
f80480de7f
Move ClDevice to a separate file
...
Related-To: NEO-3938
Change-Id: I275b9285b70dac2c9bc52878f6e517e4f3e083b3
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2020-01-30 12:46:10 +01:00
Jaroslaw Chodor
33ac782f03
Allow empty kernel arg info
...
Change-Id: I0e45e342148dfb4dceca1e7fdba885280e4ab597
2020-01-29 17:58:22 +01:00
Jaroslaw Chodor
2e64471f58
Fixing regression in arg_info tests
...
Resolves: NEO-4188
Change-Id: I375d0efc084b95d4a93a987b87d9e5635d7ec26b
2020-01-25 19:09:21 +01:00
Jaroslaw Chodor
b74d502052
Moving patchtokens decoder to core
...
Change-Id: I61d9f3ec7a1bca55df5b3b8c1884014acff1a4c0
2020-01-25 15:16:01 +01:00
Jaroslaw Chodor
f057712fa7
Program refactor
...
* decouple program_info
* move global allocations relocation to linker
* remove obsolete tests
* initial cleanup to kernel_info kernelInfo
* unified patchtoken validation
Change-Id: I0567cd6d607b4f3cf44e6caf33681f6210760f76
2020-01-25 10:56:30 +01:00
Filip Hazubski
8d34f40aad
Add clGetKernelSuggestedLocalWorkSizeINTEL
...
This function can be used to query local work size that would be used in
case of querying ND range kernel with local_work_size set to NULL.
Change-Id: I86ac7c97cffb6c3e11b673a28285739edfabb4a6
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2020-01-23 13:50:37 +01:00
Filip Hazubski
82bc594af0
Add clEnqueueNDRangeKernelINTEL API
...
Related-To: NEO-2712
Change-Id: If1d16d9d626871a9dc4b19282f9edc5786ffa398
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2019-12-04 17:11:28 +01:00
Mateusz Jablonski
54f65c0243
Move headers to core
...
- hw_info
- hw_cmds
- kmd_notify_properties
- completion_stamp
- bxml_generator_glue
Related-To: NEO-3982
Change-Id: I3ed3ef81f42596f381e60c19250f6eb1296d47a4
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
2019-12-02 14:20:45 +01:00
Jaroslaw Chodor
355e8d3e5a
[1/N] Program refactor - decouple from patchokens
...
Change-Id: I63bbf6c31a5db9e788124f22b6105e65c16c86d4
2019-11-25 19:46:21 +01:00
Mateusz Jablonski
e7ee6daaa0
Remove runtime/gen_common from include paths
...
Change-Id: I4d1f9e64e0f4099e7903234e62b070ad4235347a
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
2019-11-19 13:37:34 +01:00
Igor Venevtsev
63fd26f6d6
Always specify rootDeviceIndex for graphics memory allocations
...
Related-To: NEO-2941
Change-Id: Ia2362fd6b4e72ede02919152475f40b3edbc3658
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
2019-11-15 15:14:41 +01:00
Dunajski, Bartosz
9d6dcd6fff
Use Kernels maxKernelWorkGroupSize to compute WG size
...
Change-Id: I947b5612f36cd2437e1ead98712c914ffe4b5b15
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
2019-09-17 08:39:05 +02:00
Jim Snow
4360aff03c
Move runtime/helpers/aligned_memory.h to core/helpers
...
Signed-off-by: Jim Snow <jim.m.snow@intel.com>
Change-Id: I15de094c51d4eb18bfff4d17fd34e817b5525fda
2019-08-06 23:56:24 +02:00
Mrozek, Michal
926c7a2a97
Detect read only for arguments with const qualifier.
...
- This will catch __global const *int allocations as read only.
Change-Id: I0d128ba7c31d476d1f144233e1c3dec370f9f550
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
2019-08-01 10:16:58 +02:00
Mrozek, Michal
c9e25a0faf
Mark constant arguments as read only in kernel argument info.
...
Change-Id: Icf49d9da060a144bc73e580ab77245e580e4812d
Signed-off-by: Mrozek, Michal <michal.mrozek@intel.com>
2019-07-31 12:57:35 +02:00
Raiyan Latif
ca74489172
Move string.h to core helpers
...
Change-Id: Ibaaab077ef2867b5e0db3bd215c261de9294063f
Signed-off-by: Raiyan Latif <raiyan.latif@intel.com>
2019-07-19 07:21:00 +02:00
Jaime Arteaga
b98b51b0d9
Move ptr.h to core folder
...
Change-Id: Icf0db7c767b2b1ea44fccc02b135f0f6c1f78c8f
Signed-off-by: Jaime Arteaga <jaime.a.arteaga.molina@intel.com>
2019-05-29 00:11:34 -07:00
Maciej Plewka
f2a8fc7ea9
Print_formatter refactor
...
Change-Id: Icb03697281b009c853d91a63d5d21ffcde545a8f
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
2019-05-23 21:37:50 +02:00
Dunajski, Bartosz
0f87e9aa1a
Rename HardwareInfo members
...
Change-Id: I85f56b677bafdd75dd958b488522393fc18b68af
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
2019-05-09 09:13:55 +02:00
Dunajski, Bartosz
bb80d327c7
Move HardwareInfo ownership to ExecutionEnvironment [1/n]
...
Change-Id: I5e5b4cc45947a8841282c7d431fb69d9c397a2d4
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
2019-05-08 16:11:01 +02:00
Maciej Plewka
9e52684f5b
Change namespace from OCLRT to NEO
...
Change-Id: If965c79d70392db26597aea4c2f3b7ae2820fe96
Signed-off-by: Maciej Plewka <maciej.plewka@intel.com>
2019-03-26 15:48:19 +01:00
Mateusz Jablonski
c0325b5d19
Don't copy memory to allocation if allocation has no storage
...
Change-Id: I3238bec02e5c1ec5877537318bb563e3d0f3799d
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
2019-03-12 09:44:17 +01:00
Mateusz Jablonski
5b2d13765a
Move logic of copying ISA to separated method
...
Change-Id: I2c5fd3004fa41ed1bf1cf3d54741756f546f6941
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
2019-03-04 09:21:15 +01:00
Filip Hazubski
8b57d28116
clang-format: enable sorting includes
...
Include files are now grouped and sorted in following order:
1. Header file of the class the current file implements
2. Project files
3. Third party files
4. Standard library
Change-Id: If31af05652184169f7fee1d7ad08f1b2ed602cf0
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
2019-02-27 11:50:07 +01:00
Mateusz Jablonski
f157943610
Allocate internal allocations through preferred pool
...
Change-Id: Ib17431ceefc1eb72f86625e0998f679baaa7cb0d
Signed-off-by: Mateusz Jablonski <mateusz.jablonski@intel.com>
2019-01-30 11:18:15 +01:00
Artur Harasimiuk
40146291ad
Update copyright headers
...
Updating files modified in 2018 only. Older files remain with old style
copyright header
Change-Id: Ic99f2e190ad74b4b7f2bd79dd7b9fa5fbe36ec92
Signed-off-by: Artur Harasimiuk <artur.harasimiuk@intel.com>
2018-09-20 18:02:35 +02:00
Cetnerowski
8647e0c349
Improve KernelInfo handling:
...
Remove wrapper for KernelInfo constructor
Switch to unique pointer where possible
Change-Id: Ib3f323e34836e1d189d836fd539ab45518609610
2018-08-23 13:55:28 +02:00
Mrozek, Michal
d2817427af
Remove createInternalGraphicsAllocation function.
...
- Route directly to allocate32BitGraphicsMemory
Change-Id: Ia6872bae655c530ff06b0ec270f419ca91d005ce
2018-05-21 04:11:43 +02:00
Mateusz Jablonski
835a1da175
Update kernel allocation when substitute kernel heap
...
Change-Id: Iee02a93d4e10c7b32fae56ffa61c90d8617d6ec9
2018-04-05 10:49:40 +02:00
Mateusz Jablonski
79a0e3253e
Enable transforming image 3d to image 2d array
...
Change-Id: I8fdc6899780481bdebeaf858a330e9dea822bda3
2018-04-05 09:10:54 +02:00
Hoppe, Mateusz
cc6fa3d1e1
Kernel source debugging support 1/n
...
- new patch token
- program debug compilation flag
- sip kernel new methods for querying bti and debug
surface size
Change-Id: Icaddd15f269c4b76efdf926f2e346aa61cbaae02
2018-03-13 08:01:29 +01:00
Mrozek, Michal
f90ebac12a
Clean obsolete code.
...
Change-Id: I9551f7217924c7ea8f44a3322fc3096252c4d6f7
2018-02-23 08:10:12 +01:00
Mateusz Jablonski
ea021f8d69
Cmake refactor part 1: fix dependencies with including os_inc.h
...
Remove some not needed includes
Change-Id: I158ad663ccfcec4822e3768df9d05090c5e096f9
2018-02-08 09:40:40 +01:00
Mrozek, Michal
ee250be942
Fix num thread per slice computation.
...
- It should use thread count not EU count.
- change variable name to reflect that we work on sublices.
- fix test description, add missing test
- change hasBarrier variable to be boolean
Change-Id: I627bdf17b661d2f9b5eb3d8cd6ca53eba5d46b81
2018-01-16 13:06:31 +01:00
Brandon Fliflet
7e9ad41290
Initial commit
...
Change-Id: I4bf1707bd3dfeadf2c17b0a7daff372b1925ebbd
2017-12-21 00:45:38 +01:00