intel/compute-runtime
1
0
Fork 0
mirror of https://github.com/intel/compute-runtime.git synced 2025-12-25 21:42:53 +08:00
Code Issues Packages Projects Releases Wiki Activity
3,625 Commits 42 Branches 655 Tags
1856248e7eef04bc8aebca30dac361d7d12b4110
Commit Graph

490 Commits

Author SHA1 Message Date
Filip Hazubski
f14793895e Fix SyncBufferHandler test 
Change-Id: I281d696b2b349c2189caa28e3d8a29a001e514cb
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-12-09 18:18:41 +01:00
Gibala
5ac1d1258c Connect UnifiedMemoryProperties with MemoryPropertiesFlags 
-Add support to SvmAllocationData
-Refactor parseMemoryProperties
-Add allocation flags

Related-To: NEO-4011
Change-Id: I3728d2319aeef983dbcc3f8702da9a303a4e2b9c
Signed-off-by: Gibala <krzysztof.gibala@intel.com>
 2019-12-09 14:23:46 +01:00
Dunajski, Bartosz
b544b2da60 Remove redundant CommandQueue member 
Change-Id: I2ee338a3134cd81d6de7ecbed47c049dfbbae5aa
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-09 13:13:45 +01:00
Jaroslaw Chodor
72a1542140 [2/N] Program refactor - gather compiler options 
Change-Id: I0a614be73fbd87184be2dfea407582a58c27b0bc
 2019-12-06 22:17:19 +01:00
Dunajski, Bartosz
32d1869d4f Pass svm allocations during SVMMemcpy 
Change-Id: Ief9e5f6b96f870ac9bf152c88f0d21ff4654ac21
 2019-12-06 15:13:32 +01:00
Kamil Kopryk
baba643844 Added support for stateless enqueueSVMMemFill 
Change-Id: Ieaef91def4097c7dce618e24917c4f55cb2b914c
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-12-06 15:01:29 +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
Dunajski, Bartosz
dfc50f3a75 Move gmm_helper to core 
Change-Id: I31ca317d10697ab884e04f443c8ccfdd6ca9d2ae
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-04 15:25:32 +01:00
Dunajski, Bartosz
ec21f06427 Move GMM-OCL types conversions to new helper + includes cleanup 
Change-Id: I13e5917a32a5cd894ee42a848407fe20bf1daa06
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-04 10:42:49 +01:00
Kamil Kopryk
ec63a03337 Added support for stateless enqeueueSVMMemcpy 
Change-Id: I1690735b7888b29572b75756d38698305805b7cb
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-12-03 19:00:47 +01:00
Dunajski, Bartosz
1ecad5faed Move IndirectHeap to core and improve unit tests 
Change-Id: If7e329fc12fe934eb0f6b1762d3b0d86aab287e6
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-03 15:06:27 +01:00
Dunajski, Bartosz
614156dd8b Move cache_policy to core 
Change-Id: I16be70d15f329117539fe6dfcc07c6dc10d54977
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-03 14:53:49 +01:00
Dunajski, Bartosz
0527c9113c Disable TimestampPacket optimizations in Aub/Tbx mode 
Avoid removing semaphores and reusing returned tags

Change-Id: Ic26167953c5d5a9ccceaae49f4921af11a375fab
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-12-02 15:38:13 +01:00
Adam Cetnerowski
8f46761262 ULT renaming: Flush tests 
Related-To: NEO-2236

Change-Id: I86fbac1205dba63d4b8918d4eeec215428bb5949
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-12-02 09:08:33 +01:00
Filip Hazubski
0193b3ea69 Change maxNBitValue to a constexpr function 
Now maxNBitValue can be used with run time variables.

Change-Id: I323071400305e05e6303a33e24e90c521246d73f
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-28 14:40:16 +01:00
Adam Cetnerowski
0ba31a46cb ULT renaming: Write image & buffer tests 
Related-To: NEO-2236

Change-Id: Ida866017f17795140817f9fbdca80def8d00e4c8
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-28 14:27:47 +01:00
Dunajski, Bartosz
3f43224e1b Make EXTERNAL_HOST_PTR one time aub writable 
Change-Id: Ib8ac51ebad8997a0b10431d8c78239dc38beb616
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-28 09:25:07 +01:00
Zbigniew Zdanowicz
7781650586 Simplify Preemption interface and get device preemption once 
Change-Id: Iaab9b9b60a71651125df27dece1a68e9c9435143
Signed-off-by: Zbigniew Zdanowicz <zbigniew.zdanowicz@intel.com>
 2019-11-27 16:28:45 +01:00
Adam Cetnerowski
a0cbc21919 ULT renaming: Finish tests 
Related-To: NEO-2236

Change-Id: I2233ce516b6e8e09191ccdb0733f53fee0a29b6d
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-27 14:54:46 +01:00
Adam Cetnerowski
b00a058173 ULT renaming: Unmapping Memory Object tests 
Related-To: NEO-2236

Change-Id: Icf6c3340bef9a7eff2e6715168678ef7ceb2c59d
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-27 12:47:43 +01:00
Pawel Wilma
472a75912d Return error code from submit() to application. 
Related-To: NEO-3741

Change-Id: I0e0ff6606eb6a8a77673949955c8e799689017b6
Signed-off-by: Pawel Wilma <pawel.wilma@intel.com>
 2019-11-26 12:42:47 +01:00
Adam Cetnerowski
b2877d3725 ULT renaming: Enqueue SVM tests 
Related-To: NEO-2236

Change-Id: I9c569846a5a0f16b65566d1d5f52cc98b49b19f7
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-26 08:35:27 +01:00
Dunajski, Bartosz
7727cb230a Add missing override 
Change-Id: I47bbe57121534cc24b3fb0969a57e5fead498040
 2019-11-25 11:13:28 +01:00
Adam Cetnerowski
c5229e9514 ULT renaming: Read image tests 
Related-To: NEO-2236

Change-Id: I426f311702630db48f952d5a265804839db162d2
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-22 20:36:17 -08:00
Adam Cetnerowski
c2ab0b1b94 ULT renaming: Write buffer rect tests 
Related-To: NEO-2236

Change-Id: I1ded69858ed6998fe03669383fd697129488a0b7
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-22 16:41:47 +01:00
Dunajski, Bartosz
bd3acceacd Improve aux translation mode unit tests 
Change-Id: Ie8965b1da2a1c8926f59c557e55266379b85271f
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-22 11:57:48 +01:00
Gibala Krzysztof
de83356b10 Program all semaphores dependencies 
Related-To: NEO-3902
Change-Id: I5d8581cf4d1d50bc63626046972336b92af2a071
Signed-off-by: Gibala Krzysztof <krzysztof.gibala@intel.com>
 2019-11-22 08:53:59 +01:00
Dunajski, Bartosz
08ceaf432a Enable blit operation on enqueue copy buffer 
Change-Id: Ie9571344a9b1e2a783c59955a68094f2868f36ee
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-21 20:54:02 +01:00
Kamil Kopryk
5ecb9905c9 Add support for stateless copy image to buffer 
Change-Id: I91d1a45d87a5984e0bb7fdb302a716ffcea7bfc8
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-19 17:17:12 +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
Dunajski, Bartosz
2d5169cf65 Setup enqueue dependencies in blocked path 
Change-Id: Ia6d549924e3e557bae74dbdac691987450cbd3b7
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-19 08:55:55 +01:00
Kamil Kopryk
9d705e7905 Add support for stateless copy buffer to image 
Change-Id: I494a64ecea8ff184626eeee3069de16f37e5b24b
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-18 14:06:06 +01:00
Dunajski, Bartosz
8e945e7919 Improve TimestampPackets handling in blocked path 
Change-Id: Idf381a8750cebec6196eb299661dda892e11144d
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-18 09:25:56 +01:00
Dunajski, Bartosz
46b5513028 Initial Blit aux translation support 
Change-Id: I67fb71be57cff28a3736d5ffb9e1c39b2498feb8
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-16 11:42:10 +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
Filip Hazubski
5f021afd6d Move HwHelper to core directory 
Change-Id: I2c78a8b737ee8e61b917b4918da37e77bbd9fe34
Signed-off-by: Filip Hazubski <filip.hazubski@intel.com>
 2019-11-15 14:06:40 +01:00
Adam Cetnerowski
7311cf9fde ULT renaming: Read Buffer Rectangle tests 
Related-To: NEO-2236

Change-Id: I72081fe65bf4f2fd96e00ab3670862177be88fa5
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-15 10:59:12 +01:00
Michal Mrozek
e7901775a8 Improve enqueue kernel error handling. 
- Do not allow to enqueue parent kernel if there is no device queue.

Change-Id: I0f06b8ed2387fc87abd652653f2c8bb8c4939a12
Signed-off-by: Michal Mrozek <michal.mrozek@intel.com>
 2019-11-13 19:29:19 +01:00
Dunajski, Bartosz
b6015b5293 Add TimestampPacketDependencies helper 
Change-Id: I3945ac8e495baf442b4f892ba415f939e8d316da
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-13 16:04:48 +01:00
Dunajski, Bartosz
80407aec15 Program barrierTimestampPacketNodes only on first unblocked command 
Change-Id: I8ebba9f8326e3da2365c001b0c350efb372a3774
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-12 15:37:51 +01:00
Adam Cetnerowski
b855852500 ULT renaming: Read buffer event tests 
Related-To: NEO-2236

Change-Id: I25282c327180629020fdebc2aeeb321543455dc1
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-12 12:31:53 +01:00
Dunajski, Bartosz
af8ce96ab4 Add move logic to TimestampPacketContainer 
Change-Id: Ib666fd57b4ca9123e324a82c3e648b0da49abffc
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-12 08:50:00 +01:00
Dunajski, Bartosz
ad2b8a0bbe Allow dispatching multiple blit commands with single flush 
Change-Id: I57ea32dfa8cfd89ec37fc2f1f82ee6f72598c18a
Signed-off-by: Dunajski, Bartosz <bartosz.dunajski@intel.com>
 2019-11-08 14:35:44 +01:00
Kamil Kopryk
b2fbab7f28 Add support for stateless write buffer rect 
Change-Id: Id10c97ff2b7c07ca828b17d6bcbc36e97fadfb83
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-07 16:13:04 +01:00
Kamil Kopryk
0ef81b2bc0 Add support for stateless read buffer rect 
Change-Id: I794be4cacaa9de661c0c7e6ec67da85b0d5eed9a
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-07 16:07:03 +01:00
Adam Cetnerowski
3f42625dcc ULT renaming: Migrate Mem Objects tests 
Related-To: NEO-2236

Change-Id: If6469c42fd906d115cfa87adc3df9e97409d32f8
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-07 15:30:01 +01:00
Adam Cetnerowski
7e6b47cc14 ULT renaming: Enqueue Marker tests 
Related-To: NEO-2236

Change-Id: Ib907867e6b711266b8588934458291672391d208
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-07 11:59:53 +01:00
Kamil Kopryk
011701ee5e Fix for forceStateless check 
Change-Id: Ic1d4787c3d8c7bdd70f13451d703bbc9958af7c7
Signed-off-by: Kamil Kopryk <kamil.kopryk@intel.com>
Related-To: NEO-3314
 2019-11-07 08:28:51 +01:00
Adam Cetnerowski
9b87eabadc ULT renaming: Media kernel tests 
Related-To: NEO-2236

Change-Id: I7c38b860128e2e07c77e4ee194247eb054ca763f
Signed-off-by: Adam Cetnerowski <adam.cetnerowski@intel.com>
 2019-11-06 14:11:11 +01:00
Igor Venevtsev
684d58d2aa Make GraphicsAllocation constructors unambiguous 
Related-To: NEO-2941

Change-Id: Iedd16d0dcb4158b5e7832043289e2e6aba1549d5
Signed-off-by: Igor Venevtsev <igor.venevtsev@intel.com>
 2019-11-06 10:12:26 +01:00