11bdf0005f
[PAL] Detect if resizable bar is enabled
...
Change-Id: I54b2e878d1cf7235a848a4b243f878538e226702
2020-10-02 12:25:00 -04:00
189ec6f794
SWDEV-2 - Change OpenCL version number from 3206 to 3207
2020-10-02 03:00:03 -04:00
c8ac97a1e0
enable building cooperative directed tests on NV platform
...
Change-Id: I9a658b28010176d4f9401010b9c4b4be7ae86b92
2020-10-02 00:59:40 -04:00
a900c86746
CMakeLists.txt: Conformant package naming
...
Change-Id: I1c70559208606de8cc00909132cba38a2cc2ccd6
Signed-off-by: Cole Nelson <cole.nelson@amd.com >
2020-10-01 18:25:15 -04:00
6b4eb0a97a
[dtest] move all the cooperative related tests into one location
...
Change-Id: I9b44027d795ebfbf42f78af8e69d26ac8109692a
2020-10-01 16:01:46 -04:00
35a3304acc
rename abort in nvcc path
...
[background] There is currently a compilation issue when both hip/hip_runtime.h and hip/hip_cooperative_groups.h included
in a file and hipcc used to compile it on NV platform. The issue is that an abort is defined in hip/nvcc_detail/hip_runtime.h
and it is also defined in the CUDA cooperative groups header (/cuda/include/cooperative_groups/details/helpers.h).
this is problematic and leads to a compilation issue in hipcc on NV platform.
Change-Id: I2ab6982ac4103822a1a4a0ced942cd604d6c19c1
2020-10-01 14:28:51 -04:00
4817ec4778
fix a bug for calculating the prev_sum of MGSyncInfo struct used in multi-gpu cooperative launch
...
SWDEV-251619
Change-Id: I6566bfc9384bb4677562085991a7a01d3cea3935
2020-10-01 14:05:22 -04:00
af8426b0e4
Revert "Reduce the default size of the signal pool"
...
This reverts commit e68d671a51
2020-10-01 09:56:05 -04:00
d8404bfee9
SWDEV-2 - Change OpenCL version number from 3205 to 3206
2020-10-01 03:00:04 -04:00
1183455755
Fix Windows build
...
Change-Id: Icdc723843541a5c13503670b5f972b78db0cccbf
2020-09-30 14:40:07 -04:00
9b6d26f8b2
Add missing definitions for class static members
...
The static members __HIP_Coordinates::x, ::y and ::z must be defined
outside the class. Otherwise, linker throws `undefined reference error`
when these definitions are needed in the HIP application.
Change-Id: Iabc09744b478c22e4b13cf9824877ec9cfdd4f7a
2020-09-30 03:38:24 -04:00
deeb37412c
SWDEV-253247: add ulong and ulonglong version of__shfl*
...
Change-Id: I40ab6cfa12175f334e8392b71f567054d8256e2a
2020-09-30 01:58:22 -04:00
b35f5215b2
Layout the cooperative group related headers to target Nvidia
...
Change-Id: I530ffc72d6fae1e273b5322d508629221e11ea6f
2020-09-29 21:32:24 -04:00
d4fa2e8c80
SWDEV-253654 : Added invalid parameter checks
...
Change-Id: I8a2ae1ee6898f111aac1c68663a653cca410daec
2020-09-29 13:20:27 -04:00
3d59e050db
SWDEV-247518-fix HPC multi gpu test performance drop
...
Change-Id: I2f07d9ba183cf88b3845d8d61607a8a0462d015f
2020-09-29 12:04:40 -04:00
d0f009a0ee
Adding and populating available registers per cu value
...
Change-Id: Ide012038a9d74b20166ce1e69a9f2c0cbdce0d73
2020-09-28 05:30:23 -04:00
b26a283118
SWDEV-2 - Change OpenCL version number from 3204 to 3205
2020-09-26 03:00:04 -04:00
7da8264b7c
SWDEV-252337: Fix for V100 compilation issue
...
Change-Id: Ib57ff3ac28f0a581f395f32181974e64eca6d858
2020-09-25 21:55:22 -04:00
f93a2b03ad
SWDEV-253250-update instruction for hip sample
...
Change-Id: Iebc2887a3687e6c565999f4faf1cd4cf893e24cd
2020-09-25 13:51:19 -04:00
a680b514b3
fix a pagefault when wrong argument (extent) passed in hipMemset3D API
...
Change-Id: I779fc14ccd7c942d1ae0a938ebfd3c2e728ff761
2020-09-25 10:57:37 -04:00
4071cf1a16
SWDEV-241896 - Remove extern support in ROCclr/HIP since compiler added Texture Reference support.
...
Change-Id: I2cf27e13a53860fe11e9245c9cbdcb8bd88a7872
2020-09-25 10:20:16 -04:00
40b432f992
Avoid using sdma engine if there's none
...
Change-Id: Id8d373683f3e1667ab461b4c5b8b490377b64cc0
2020-09-25 09:48:10 -04:00
2e199bd492
Fix a crash when printf used in a kernel launched on a stream with custom CU mask
...
SWDEV-249719 - root cause: queues with custom CU mask are not inserted
into queuePool_ (i.e., queue of reusable HSA queues) of ROC device class
causing a crash when creating hostcall buffers for printf
Change-Id: Ieee7005d9a5a30b3113394ce23ee65927126d0d6
2020-09-25 09:25:19 -04:00
19acb0bfe5
SWDEV-241896 - Remove extern support in ROCclr/HIP since compiler added Texture reference support.
...
Change-Id: I1b0a7377b803b4e2b94ffef6ffd91e376fdb2b2f
2020-09-24 14:28:16 -04:00
2f3d60fc4a
Return hipMemoryTypeHost as memory type for hipHostRegistered pointer
...
Fixes SWDEV-253741
Change-Id: I42c2c9df00862157314d5767b6f175a0d2f28b47
2020-09-24 12:27:32 -04:00
3c9bbc335a
SWDEV-249870 - Short-Term solution for Pre-Compiled Headers for Online Compilation
...
Change-Id: Iec989787e546ff2eb68c4b146dc540655698b569
2020-09-24 12:18:06 -04:00
eedf4c68dc
[dtest] Additional tests for hipMallocManaged() api
...
5 scenarios were added for hipMallocManaged including negative
test.
SWDEV-238517 for enhancing hip unit tests
Change-Id: Ibba53fb64502d6df798e4e63100dcb8c5f94553f
2020-09-24 10:05:21 -04:00
0cef35c402
SWDEV-2 - Change OpenCL version number from 3203 to 3204
2020-09-24 03:00:02 -04:00
a363eeb4f4
SWDEV-253349 - Add a SKIP state for hip directed tests when HIP_BRINGUP_SKIP macro is used.
...
Change-Id: If176cf775e568d4b32982127731223fe96a38f0d
2020-09-23 16:46:21 -04:00
bd4c6ce6dc
Don't use CMAKE_SOURCE_DIR
...
Change-Id: I373e218850e72ca8fe7f76a7af3e559c485c569b
2020-09-23 13:04:05 -04:00
c70ff63d87
Correctly append CMAKE_SHARED_LINKER_FLAGS
...
Change-Id: Id207f7b7eea7420657162ed666fb4240e3b6e9a1
2020-09-23 13:04:02 -04:00
18352d189b
SWDEV-253063 - Code changes to make Image Buffer Workaround only for targets gfx 10.1
...
Change-Id: I17044a1c0775f427b9ba712eb3fd5ab21ed88b0e
2020-09-23 11:07:15 -04:00
612bfc87f2
[dtest] Tests for hipMalloc
...
1. API validation
2. Validate the memory status after hipMalloc()
3. Test repeated hipMalloc() Calls, call in multiple threads
4. Parallel hipMalloc() from parent and child processes
5. hipMalloc() from multiple processes on multiple GPUs
SWDEV-238517 for enhancing hip unit tests
Change-Id: Ie152999d7a203a51704d2888ccc1ca866a2e1b05
2020-09-23 09:20:01 -04:00
591905915a
[dtest] Tests for hipIpcGetMemHandle()
...
Tests allocation of memory on various GPUs and pass on the IPC mem handle to child process.
Child process attaches to the mem handle and uses the memory on various GPUs
SWDEV-238517 for enhancing hip unit tests
Change-Id: I7babc7725813e05d651057beef6a8bec6f62a49b
2020-09-22 23:49:30 -04:00
c197183818
use only hip compiler to compile hip cooperative groups
...
SWDEV-252377
Change-Id: I6cf749dad2bf05c2e49fed495ab2833c574c2215
2020-09-22 14:34:05 -04:00
93f5675015
Added performance test for Device concurrency
...
Change-Id: I30f4e65467613152ce86b80b13e1c9f2928da801
2020-09-22 12:59:38 -04:00
a17c4dce84
SWDEV-248163: Adding new Mandelbrot's tests - Serial vs concurrent kernel execution and mad vs fma performance results
...
Change-Id: I5118d13b40e2d17414124eebfd1b5114641db978
2020-09-22 12:58:57 -04:00
2f98dbedca
SWDEV-2 - Change OpenCL version number from 3202 to 3203
2020-09-22 03:00:03 -04:00
c74cf90c7e
SWDEV-240803 - add test for hipFuncSetSharedMemConfig
...
Change-Id: I150b65a548ee9bf8d7e079b3db2e73958747c3a0
2020-09-21 17:26:51 -04:00
e1b916260a
Fix Windows legacy LLVM build
...
The os.hpp header gets added to the include path of legacy llvm via the compiler lib. Having "windows.h" included causes a lot conflicts with LLVM headers, as they forward declare many Windows types. Best to not include it here.
Change-Id: I60c44a8d28660368f1a4a95741e1053ef3528fa1
2020-09-21 11:52:01 -04:00
2cce9170c3
CMake changes to now write to test folder
...
Change-Id: Ia898b31a09f3c59ef8e7d64253f28ae93c501277
2020-09-21 00:37:15 -04:00
d752b6d14b
Adding checks for return type compatibility with CUDA
...
Change-Id: I09b6bd9a7299f0a97ac9011ea0903a1f81e28251
2020-09-21 00:36:02 -04:00
7fd56c6f13
SWDEV-2 - Change OpenCL version number from 3201 to 3202
2020-09-19 03:00:04 -04:00
1602db4114
Fix Windows build
...
Change-Id: I8769bafba199b9258c610e51b58e454fe10a75e6
2020-09-18 18:51:25 -04:00
fdb4d45a3f
SWDEV-252542 - Fixing Win Compilation on SWDEV-241902.
...
Change-Id: I0ef196231acd8e778018bade684a10ec977261a5
2020-09-18 14:11:07 -04:00
1965939b0d
SWDEV-249486-update doxygen linked file
...
Change-Id: I90e42b83ad38323feb8d80aff136829837ef1aef
2020-09-18 13:53:01 -04:00
a6b6881c86
Amend hipBusBandwidth sample
...
Change-Id: I9230b553275146e984c6e7d9f11b76e520e14809
2020-09-18 13:45:19 -04:00
531c2c7596
Fix a warning with cooperative groups header
...
SWDEV-252413
Change-Id: Ia098464b670f26416b79cc67805b8accb6bec903
2020-09-18 13:38:47 -04:00
7462e39954
SWDEV-252542 - Fixing Win Compilation on SWDEV-241902.
...
Change-Id: If76f79002b265dccf6da4acef1ff9372d8b0a2ff
2020-09-18 12:11:56 -04:00
90c694988b
set free mem to zero avoding underflow
...
Change-Id: I964b41695fb41712624146c5959a35b37eacf52d
2020-09-18 11:56:57 -04:00
Vladislav Sytchenko
Chauncey Hui
Aryan Salmanpour
Cole Nelson
German Andryeyev
mshivama
Sarbojit Sarkar
Julia Jiang
Jatin Chaudhary
kjayapra-amd
Jason Tang
Rahul Garg
agodavar
Lakhan singh Thakur
Sumanth Tumbalam Gooty
Sourabh Betigeri
Todd tiantuo Li
Satyanvesh Dittakavi