76333 Коммитов

Автор SHA1 Сообщение Дата
Maneesh Gupta 939909e96c Disable broken test: hipC
Change-Id: I061aa125bbdc9f14bc870266ab0735593c861903
2017-02-06 13:00:50 +05:30
foreman d21a308c20 P4 to Git Change 1369347 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/05 03:00:10
SWDEV-2 - Change OpenCL version number from 2356 to 2357.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2103 edit


[ROCm/clr commit: 3d78cc9365]
2017-02-05 03:10:19 -05:00
foreman 3d78cc9365 P4 to Git Change 1369347 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/05 03:00:10
SWDEV-2 - Change OpenCL version number from 2356 to 2357.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2103 edit
2017-02-05 03:10:19 -05:00
foreman ca7a01716b P4 to Git Change 1369315 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/04 03:00:04
SWDEV-2 - Change OpenCL version number from 2355 to 2356.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2102 edit


[ROCm/clr commit: 6a684f91a6]
2017-02-04 03:15:20 -05:00
foreman 6a684f91a6 P4 to Git Change 1369315 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/04 03:00:04
SWDEV-2 - Change OpenCL version number from 2355 to 2356.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2102 edit
2017-02-04 03:15:20 -05:00
foreman a5e2d28f34 P4 to Git Change 1369302 by todli@todli-win-opencl-kv1 on 2017/02/04 00:49:06
SWDEV-107271 - Fix crash that happens when Resource::create() fails and "owner" gets cleared. This is only triggered by Conformance test Basic progvar_prog_scope_misc on Raven with 16GB memory (8GB is fine), but should be a general bug.
	http://ocltc.amd.com/reviews/r/12253

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#11 edit


[ROCm/clr commit: c2ca879dec]
2017-02-04 00:59:54 -05:00
foreman c2ca879dec P4 to Git Change 1369302 by todli@todli-win-opencl-kv1 on 2017/02/04 00:49:06
SWDEV-107271 - Fix crash that happens when Resource::create() fails and "owner" gets cleared. This is only triggered by Conformance test Basic progvar_prog_scope_misc on Raven with 16GB memory (8GB is fine), but should be a general bug.
	http://ocltc.amd.com/reviews/r/12253

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#11 edit
2017-02-04 00:59:54 -05:00
foreman 84217acb21 P4 to Git Change 1369163 by todli@todli-win-opencl-kv1 on 2017/02/03 17:19:46
SWDEV-96241 - fix OpenCL/LC build failure

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#43 edit


[ROCm/clr commit: 28f7b5b678]
2017-02-03 17:29:15 -05:00
foreman 28f7b5b678 P4 to Git Change 1369163 by todli@todli-win-opencl-kv1 on 2017/02/03 17:19:46
SWDEV-96241 - fix OpenCL/LC build failure

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#43 edit
2017-02-03 17:29:15 -05:00
Amber Lin 9dadac6dc9 Add IOMMU to performance counter table
Add IOMMUv2 to blocks returned by hsaKmtPmcGetCounterProperties(). IOMMU
information is read from sysfs.

Change-Id: I3a1c6f902f947913570a78700fc0ffc444e1dd72
Signed-off-by: Amber Lin <Amber.Lin@amd.com>
2017-02-03 14:35:27 -05:00
Amber Lin 00e295eff3 Add IOMMU to performance counter table
Add IOMMUv2 to blocks returned by hsaKmtPmcGetCounterProperties(). IOMMU
information is read from sysfs.

Change-Id: I3a1c6f902f947913570a78700fc0ffc444e1dd72
Signed-off-by: Amber Lin <Amber.Lin@amd.com>


[ROCm/ROCR-Runtime commit: 9dadac6dc9]
2017-02-03 14:35:27 -05:00
Ramesh Errabolu 7755bd5487 Refactor Device Id to Asic Type Mapping Service
Change-Id: I8969b41f7c4de9fdeee5131e2049053a486f64fb
2017-02-03 14:22:32 -05:00
Ramesh Errabolu 4a70f68afb Refactor Device Id to Asic Type Mapping Service
Change-Id: I8969b41f7c4de9fdeee5131e2049053a486f64fb


[ROCm/ROCR-Runtime commit: 7755bd5487]
2017-02-03 14:22:32 -05:00
Aditya Atluri 3937b398e9 changed __global__ attribute
1. Moved around tests and added them to HIT

Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b


[ROCm/clr commit: f009f3533d]
2017-02-03 10:53:36 -06:00
Aditya Atluri f009f3533d changed __global__ attribute
1. Moved around tests and added them to HIT

Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b
2017-02-03 10:53:36 -06:00
Aditya Atluri 6d5992d445 changed __global__ attribute
1. Moved around tests and added them to HIT

Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b


[ROCm/hip commit: 5e3d63c0a3]
2017-02-03 10:53:36 -06:00
Aditya Atluri 5e3d63c0a3 changed __global__ attribute
1. Moved around tests and added them to HIT

Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b
2017-02-03 10:53:36 -06:00
Amber Lin d4dbf562a9 Replace spaces with tabs
Thunk follows Linux kernel coding convention to use tabs instead of
spaces.

Change-Id: I4eddcfa9a0513f16c869d9cc63f9f1dae0c39f83
Signed-off-by: Amber Lin <Amber.Lin@amd.com>
2017-02-03 10:13:24 -05:00
Amber Lin 67049d7175 Replace spaces with tabs
Thunk follows Linux kernel coding convention to use tabs instead of
spaces.

Change-Id: I4eddcfa9a0513f16c869d9cc63f9f1dae0c39f83
Signed-off-by: Amber Lin <Amber.Lin@amd.com>


[ROCm/ROCR-Runtime commit: d4dbf562a9]
2017-02-03 10:13:24 -05:00
foreman 41f7a9f955 P4 to Git Change 1368828 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/03 03:00:04
SWDEV-2 - Change OpenCL version number from 2354 to 2355.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2101 edit


[ROCm/clr commit: 5615f44274]
2017-02-03 03:10:56 -05:00
foreman 5615f44274 P4 to Git Change 1368828 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/03 03:00:04
SWDEV-2 - Change OpenCL version number from 2354 to 2355.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2101 edit
2017-02-03 03:10:56 -05:00
foreman fcf63c43c8 P4 to Git Change 1368703 by todli@todli-win-opencl-kv1 on 2017/02/02 18:12:31
SWDEV-96241 - Support SDI on PAL (runtime changes)

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#23 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#16 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#42 edit


[ROCm/clr commit: 1eda218988]
2017-02-02 18:23:12 -05:00
foreman 1eda218988 P4 to Git Change 1368703 by todli@todli-win-opencl-kv1 on 2017/02/02 18:12:31
SWDEV-96241 - Support SDI on PAL (runtime changes)

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#23 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#16 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#42 edit
2017-02-02 18:23:12 -05:00
Felix Kuehling a90abcb317 Allocate paged system memory as userptr
Change-Id: I0864e678681788df37eccd9d7ebc70086e1f93bf
2017-02-02 10:32:53 -05:00
Felix Kuehling 73c7c197af Allocate paged system memory as userptr
Change-Id: I0864e678681788df37eccd9d7ebc70086e1f93bf


[ROCm/ROCR-Runtime commit: a90abcb317]
2017-02-02 10:32:53 -05:00
foreman 3db14ee4cb P4 to Git Change 1368336 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/02 03:00:03
SWDEV-2 - Change OpenCL version number from 2353 to 2354.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2100 edit


[ROCm/clr commit: 917f2935ed]
2017-02-02 03:15:42 -05:00
foreman 917f2935ed P4 to Git Change 1368336 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/02 03:00:03
SWDEV-2 - Change OpenCL version number from 2353 to 2354.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2100 edit
2017-02-02 03:15:42 -05:00
Aditya Atluri f36992067b fixed symbol memcpy issue
Change-Id: I89d7401be51d194bcbf771020ba66e3d3b6a18f8


[ROCm/clr commit: 0d4e6ae60a]
2017-02-01 17:54:59 -06:00
Aditya Atluri 0d4e6ae60a fixed symbol memcpy issue
Change-Id: I89d7401be51d194bcbf771020ba66e3d3b6a18f8
2017-02-01 17:54:59 -06:00
Aditya Atluri afb38e15de fixed symbol memcpy issue
Change-Id: I89d7401be51d194bcbf771020ba66e3d3b6a18f8


[ROCm/hip commit: 2790e9a448]
2017-02-01 17:54:59 -06:00
Aditya Atluri 2790e9a448 fixed symbol memcpy issue
Change-Id: I89d7401be51d194bcbf771020ba66e3d3b6a18f8
2017-02-01 17:54:59 -06:00
foreman 73fe771169 P4 to Git Change 1368253 by gandryey@gera-w8 on 2017/02/01 18:29:08
SWDEV-112352 - [ROCm CQE][OCLonLC][QR][G] Aborted/Segmentation fault is observed with "sub_buffers_read_write_dual_devices" of Buffers, due to CL#1364923
	- Keep system memory for multiple devices in case of possible initialization on the second device

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#41 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#9 edit


[ROCm/clr commit: a10c33ad77]
2017-02-01 18:39:14 -05:00
foreman a10c33ad77 P4 to Git Change 1368253 by gandryey@gera-w8 on 2017/02/01 18:29:08
SWDEV-112352 - [ROCm CQE][OCLonLC][QR][G] Aborted/Segmentation fault is observed with "sub_buffers_read_write_dual_devices" of Buffers, due to CL#1364923
	- Keep system memory for multiple devices in case of possible initialization on the second device

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#41 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#9 edit
2017-02-01 18:39:14 -05:00
Amber Lin 72b842a6dc Sync up gfx803 DIDs with KFD
Add gfx803 10/11 device IDs that were recently added to KFD.

Change-Id: Id40b117ae47bacedefa6e333fdfdf58dea92cd2d
Signed-off-by: Amber Lin <Amber.Lin@amd.com>
2017-02-01 12:05:24 -05:00
Amber Lin e4e6d49bfa Sync up gfx803 DIDs with KFD
Add gfx803 10/11 device IDs that were recently added to KFD.

Change-Id: Id40b117ae47bacedefa6e333fdfdf58dea92cd2d
Signed-off-by: Amber Lin <Amber.Lin@amd.com>


[ROCm/ROCR-Runtime commit: 72b842a6dc]
2017-02-01 12:05:24 -05:00
foreman d53338df44 P4 to Git Change 1367969 by gandryey@gera-lnx-rcf-lc on 2017/02/01 11:53:10
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- Disable ROCr copy buffer and use runtime kernel to avoid  HW hangs in integer_ops.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/blit.hpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#29 edit


[ROCm/clr commit: c0d4edda9d]
2017-02-01 12:03:40 -05:00
foreman c0d4edda9d P4 to Git Change 1367969 by gandryey@gera-lnx-rcf-lc on 2017/02/01 11:53:10
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- Disable ROCr copy buffer and use runtime kernel to avoid  HW hangs in integer_ops.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/blit.hpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#29 edit
2017-02-01 12:03:40 -05:00
foreman b71d37e251 P4 to Git Change 1367952 by gandryey@gera-w8 on 2017/02/01 11:11:26
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- Back out changelist 1367810. A hang was delayed, but still occured much later in the test.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#40 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#16 edit


[ROCm/clr commit: c36d89754a]
2017-02-01 11:21:13 -05:00
foreman c36d89754a P4 to Git Change 1367952 by gandryey@gera-w8 on 2017/02/01 11:11:26
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- Back out changelist 1367810. A hang was delayed, but still occured much later in the test.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#40 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#16 edit
2017-02-01 11:21:13 -05:00
foreman df17314d2e P4 to Git Change 1367882 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/01 03:00:05
SWDEV-2 - Change OpenCL version number from 2352 to 2353.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2099 edit


[ROCm/clr commit: 3ee45f2c08]
2017-02-01 03:07:06 -05:00
foreman 3ee45f2c08 P4 to Git Change 1367882 by johtaylo@johtaylo-jtincrementor-increment on 2017/02/01 03:00:05
SWDEV-2 - Change OpenCL version number from 2352 to 2353.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2099 edit
2017-02-01 03:07:06 -05:00
foreman 1c12ea1371 P4 to Git Change 1367875 by smekhano@stas-mwamba-rocm on 2017/02/01 01:33:12
SWDEV-105835 - ROCm OpenCL: add -amdgpu-internalize-symbols to BE

	The option -amdgpu-internalize-symbols allows to drop unused symbols from program,
	functions and global variables. This saves compile time and object size, a lot in
	case of a big program.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#33 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#55 edit


[ROCm/clr commit: df22dc2a47]
2017-02-01 01:41:59 -05:00
foreman df22dc2a47 P4 to Git Change 1367875 by smekhano@stas-mwamba-rocm on 2017/02/01 01:33:12
SWDEV-105835 - ROCm OpenCL: add -amdgpu-internalize-symbols to BE

	The option -amdgpu-internalize-symbols allows to drop unused symbols from program,
	functions and global variables. This saves compile time and object size, a lot in
	case of a big program.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#33 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocprogram.cpp#55 edit
2017-02-01 01:41:59 -05:00
Jay Cornwall 9e575ea96a Add support for ARM
- Build system fixes
- No user-mode high-precision timer by default, use clock_gettime
- Use C11 aligned_alloc pending C++17 std::aligned_alloc

Change-Id: I268365bdfd11d1e817a89584b9e086ee5b86e1dc
2017-01-31 16:43:49 -08:00
Jay Cornwall 7b45ebfe7f Add support for ARM
- Build system fixes
- No user-mode high-precision timer by default, use clock_gettime
- Use C11 aligned_alloc pending C++17 std::aligned_alloc

Change-Id: I268365bdfd11d1e817a89584b9e086ee5b86e1dc


[ROCm/ROCR-Runtime commit: 9e575ea96a]
2017-01-31 16:43:49 -08:00
foreman 01482a67c9 P4 to Git Change 1367810 by gandryey@gera-w8 on 2017/01/31 19:02:27
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- Make HSA copy call lock protected, due to a possible race condition and HW hangs in integer_ops long_math test

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#39 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#15 edit


[ROCm/clr commit: a7a4a6dbad]
2017-01-31 19:09:43 -05:00
foreman a7a4a6dbad P4 to Git Change 1367810 by gandryey@gera-w8 on 2017/01/31 19:02:27
SWDEV-112171 - [ROCm CQE][OCLonLC][QR][G] System hangs/Failures observed with few WF conf tests, due to CL#1364923
	- Make HSA copy call lock protected, due to a possible race condition and HW hangs in integer_ops long_math test

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocblit.cpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#39 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#15 edit
2017-01-31 19:09:43 -05:00
foreman 9e93e41146 P4 to Git Change 1367466 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/31 03:00:05
SWDEV-2 - Change OpenCL version number from 2351 to 2352.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2098 edit


[ROCm/clr commit: b0862beab2]
2017-01-31 03:06:32 -05:00
foreman b0862beab2 P4 to Git Change 1367466 by johtaylo@johtaylo-jtincrementor-increment on 2017/01/31 03:00:05
SWDEV-2 - Change OpenCL version number from 2351 to 2352.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2098 edit
2017-01-31 03:06:32 -05:00
Jay Cornwall 7e0a5f9c00 Add support for gfx900
- Route AQL doorbell directly to HW doorbell
- Reuse precompiled Gfx8 shaders on Gfx9 (ISA is compatible)
- Add a warning for unimplemented code cache invalidation

Change-Id: I92096584a1404e35779c96ae6bdc3e0e7fd04721
2017-01-30 16:36:28 -06:00