Commit Graph

4957 Commits

Author SHA1 Message Date
agodavar 52c79e6b63 SWDEV-255853: CUDA device P2P attributes
Change-Id: I7deffd04101b565f68a72a179f9faeaa22cab97d


[ROCm/clr commit: e65bbb0329]
2020-10-13 05:32:29 -04:00
agodavar 815e10863c SWDEV-254909:Support for missing texture/array cuda driver types
Change-Id: I9c769f6335ec3e7feacaa8929719c666bff91934


[ROCm/clr commit: fae443cb36]
2020-10-13 05:30:31 -04:00
Freddy Paul 2f1964292f HIP:Break dependency to rocm-dev package
Check for rocm_agent_enumerator instead of rocminfo or
.info/version.

Change-Id: I1718bd4f70b3e527ea3afe19c1a685ab7ed70808


[ROCm/clr commit: 5a46d80682]
2020-10-12 17:53:53 -04:00
agodavar de8da71c9a SWDEV-254185 - Added support to pass include headers to hipRTC
Change-Id: Ia19e6806a476d3c6ecd3e9a89c3ed72953a4900c


[ROCm/clr commit: 7d67573a4f]
2020-10-12 06:04:14 -04:00
Tao Sang f1cc6bef64 Revert "Make directed_test support static libs"
This reverts commit a47392be9b.

Reason for revert: <INSERT REASONING HERE>

Change-Id: Ib2d1084ea21461f70f96f95c6025a08f88288357


[ROCm/clr commit: 0d1cf31eb1]
2020-10-12 00:01:13 -04:00
Sameer Sahasrabuddhe 4a1c0fca7f Do not inline the body of __assert_fail()
The device side assertion calls printf to write out a message. In the
device compiler, printf is expanded into a series of hostcalls that
transmit the printf payload to the host. This expansion increases the
length of the kernel, resulting in sub-optimal compilation. The
solution is to ensure that the assert() implementation is not inlined
into the kernel.

Change-Id: Ia3a075461a755cf007218f262b0863e1926c76aa


[ROCm/clr commit: 160dfb5a1f]
2020-10-10 01:03:04 -04:00
Yaxun (Sam) Liu cd76837c2e Disable wave64 support on GFX10 for HIP
Change-Id: Ie3d4fe91516167ea26ce704689b6b6f1951a7521


[ROCm/clr commit: 147f064d31]
2020-10-09 17:02:56 -04:00
Tao Sang a47392be9b Make directed_test support static libs
1.Make directed_test apps linked against static libs
of hip, rocclr, rocr, roct and amd_comgr.
2.Remove custom_target amdhip64_static_combiner.
3.Support EXCLUDE_HIP_LIB_TYPE <static|shared>.
4.Simplify argument list parsing.
5.Fix hip_pch.o missing issue in samples' build.
6.Fix some original small bugs.

Change-Id: I30f5e65367613152ce86b80b13e1c9f2a28da803


[ROCm/clr commit: 36c5679efc]
2020-10-08 22:46:58 -04:00
Jason Tang b196722b7f Add hipStreamSynchronize to hipModuleLoadDataMultThreadOnMultGPU test
hipStreamDestroy() by definition doesn't guarantee waiting for all stream operations.

Change-Id: Ibfd21c48d71741ebcbcb9898c8b5ac235bdc570b


[ROCm/clr commit: f2c2fd3d09]
2020-10-08 11:06:39 -04:00
Payam 03fb2472ab Cleaning lintian warning SWDEV-247996 Part1
Change-Id: Ie024912b65125c3e14ecc278ac12e07912df6354


[ROCm/clr commit: 95bef523fe]
2020-10-08 05:44:58 -04:00
German Andryeyev d97ee5d52a Use more managed memory interfaces
Add extra API calls for managed memory: hipMemAdvise, hipMemPrefetchAsync,
hipMemRangeGetAttribute

Change-Id: Ifb09744acdf7582d278453707373c89c30e3ed03


[ROCm/clr commit: 4ee6d78763]
2020-10-07 16:45:25 -04:00
sumanthtg ceb9b66602 [dtest] Tests for atomicAdd/atomicAddnoRet
Positive and negative test cases for atomicAdd and
AtomicAddnoRet device functions

SWDEV-238517 for enhancing hip unit tests

Change-Id: Id20ba2550d20f224004f105cdcd087002cb80e56


[ROCm/clr commit: 00d46218b7]
2020-10-07 13:20:12 -04:00
sumanthtg 754936e9e9 [dtest] Additional tests for hipOccupancyMax APIs
Additional tests for following APIs
- hipOccupancyMaxActiveBlocksPerMultiprocessor
- hipOccupancyMaxPotentialBlockSize

SWDEV-238517 for enhancing hip unit tests

Change-Id: Ib9441c1366f46a082e10eb1a572bc7d8ebe1ee37


[ROCm/clr commit: 4eb65d58dd]
2020-10-07 13:19:06 -04:00
Sourabh Betigeri c8d913a3d8 SWDEV-247768: Added new perf test - SampleRate
Change-Id: I3aee07dff3759a0ac56a1afb384168bb94394187


[ROCm/clr commit: acdc435e77]
2020-10-06 12:46:13 -04:00
Sarbojit Sarkar 1dee6f664b [perf]hipMalloc perf optimization
Change-Id: I9cd1d29205cb0c9938d26bb8e336fc9fe8a262ed


[ROCm/clr commit: a3b44b5f75]
2020-10-06 12:22:57 -04:00
Vladislav Sytchenko 4a6f033fd2 Change __HIP_ENABLE_PCH to be an option
Currently all the logic checks if __HIP_ENABLE_PCH is set, so setting it
to OFF will still enable PCH.

Switching __HIP_ENABLE_PCH to be a CMake option will enable correct
build behaviour.

Change-Id: I77a663589ffb5f2595c6ad3d144eb9466adcf250


[ROCm/clr commit: 8034467ec3]
2020-10-06 11:17:47 -04:00
kjayapra-amd 78fd06679b SWDEV-254363 - Checks to make sure kernel is launched on the same device as it was launched.
Change-Id: I2f273a70b1a5fc0e9fc9c6144eabd32466ff4e59


[ROCm/clr commit: 40322a9f1c]
2020-10-06 08:38:09 -04:00
Rahul Garg 8e268b9170 Remove libhip_hcc references
These were added in commit b2e0df3845.

Change-Id: I5815c90bb83ac74730f6bce114eb353f54b86670


[ROCm/clr commit: 2a5d39cd3b]
2020-10-06 04:29:35 -04:00
Sarbojit Sarkar 8587ec2976 SWDEV:253548 : remove gfx-arch macros
Change-Id: I1ef0b4e080c15a9c6228f48ecd6a65b134d0a72d


[ROCm/clr commit: 3f0e33adb5]
2020-10-06 01:15:58 -04:00
Yaxun (Sam) Liu f3663d440c Fix warpSize for gfx10
Change-Id: I8029ebeb91db1efa8e166ad349aaae6364e8069d


[ROCm/clr commit: 71586b02e3]
2020-10-05 20:45:07 -04:00
Rahul Garg b022db2663 Bump version to 3.10
Change-Id: I7410996510fa24d2db0a4ecb2a2642e2e95058cf


[ROCm/clr commit: 9f81811fd2]
2020-10-05 20:26:38 -04:00
Vladislav Sytchenko 7b635ae18c Revert "Revert "Merge branch 'amd-master-next' into amd-npi-next""
This reverts commit 0627e8783b.

Reason for revert: <INSERT REASONING HERE>

Change-Id: I92ceb171e31026ed1864704cef2fc1497b883ef9


[ROCm/clr commit: d5aa0f607d]
2020-10-05 13:20:58 -04:00
Vladislav Sytchenko 0627e8783b Revert "Merge branch 'amd-master-next' into amd-npi-next"
This reverts commit 6c6299acb2.

Reason for revert: <INSERT REASONING HERE>

Change-Id: I53322718dadde2c98f96140b8e260ec7ee9ef721


[ROCm/clr commit: 9142674ef0]
2020-10-05 13:02:39 -04:00
German Andryeyev 913d257803 Fix error codes in HMM interfaces
Change-Id: I16490c575f2840b1116a4135431a611cf812f3a4


[ROCm/clr commit: ef5d9bd562]
2020-10-05 12:54:16 -04:00
Vladislav Sytchenko 6c6299acb2 Merge branch 'amd-master-next' into amd-npi-next
Change-Id: I0587f67e28cec51c2ae753e986d2c7ce21db271e


[ROCm/clr commit: d7c02619d6]
2020-10-05 09:51:06 -04:00
Jatin Chaudhary 284e6245d6 Use availableRegistersPerCU_ to populate number of registers
Change-Id: I58f2323bf454f910d22ab31f05aa3024a3d1106f


[ROCm/clr commit: c9d996a0a8]
2020-10-05 00:33:27 -04:00
mshivama d3bcef604a Fix bug reported in SWDEV-251619
Unit testing of CG threadRank api in multi-grid environment requires
some changes as grid id of particular device is not known apriori.

Change-Id: Ie7941a09337653f3ada5eedfb7c64a93a234498b


[ROCm/clr commit: 9c86cdb89d]
2020-10-02 13:39:10 -04:00
Pruthvi Madugundu 41e2601b0d Update to the REGEX in hip-config.cmake
- Matching the output "hipcc --version" for Installed directory
  to get the llvm compiler path, wasnt done properly.
- Adding fallback for HIP_CLANG_ROOT on ROCM_PATH if defined in env
- Changed the mode of get_filename_component to DIRECTORY

Signed-off-by: Pruthvi Madugundu <pruthvi.madugundu@amd.com>
Change-Id: Ia38e234f34cabb5b419906c7094b327083292b0e


[ROCm/clr commit: 5f667bf4e8]
2020-10-02 13:03:49 -04:00
Srinivasan Subramanian 04c782ad9a hipcc doesn't find libhsakmt without ldconf entries
Signed-off-by: Srinivasan Subramanian <srinivasan.subramanian@amd.com>
Change-Id: Iea6a43786f05c9e44dcf863f4f96a53f81384dbd


[ROCm/clr commit: 8b889ad26e]
2020-10-02 12:55:00 -04:00
Aryan Salmanpour e9ed860cc1 enable building cooperative directed tests on NV platform
Change-Id: I9a658b28010176d4f9401010b9c4b4be7ae86b92


[ROCm/clr commit: c8ac97a1e0]
2020-10-02 00:59:40 -04:00
Cole Nelson 54b171e65a CMakeLists.txt: Conformant package naming
Change-Id: I1c70559208606de8cc00909132cba38a2cc2ccd6
Signed-off-by: Cole Nelson <cole.nelson@amd.com>


[ROCm/clr commit: a900c86746]
2020-10-01 18:25:15 -04:00
Aryan Salmanpour ac20d599eb [dtest] move all the cooperative related tests into one location
Change-Id: I9b44027d795ebfbf42f78af8e69d26ac8109692a


[ROCm/clr commit: 6b4eb0a97a]
2020-10-01 16:01:46 -04:00
Aryan Salmanpour 0bc09def97 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


[ROCm/clr commit: 35a3304acc]
2020-10-01 14:28:51 -04:00
Aryan Salmanpour 67227e6f7e fix a bug for calculating the prev_sum of MGSyncInfo struct used in multi-gpu cooperative launch
SWDEV-251619

Change-Id: I6566bfc9384bb4677562085991a7a01d3cea3935


[ROCm/clr commit: 4817ec4778]
2020-10-01 14:05:22 -04:00
mshivama c0eb26b2e7 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


[ROCm/clr commit: 9b6d26f8b2]
2020-09-30 03:38:24 -04:00
Sarbojit Sarkar fc2cc1471c SWDEV-253247: add ulong and ulonglong version of__shfl*
Change-Id: I40ab6cfa12175f334e8392b71f567054d8256e2a


[ROCm/clr commit: deeb37412c]
2020-09-30 01:58:22 -04:00
mshivama 4bd3a9fb18 Layout the cooperative group related headers to target Nvidia
Change-Id: I530ffc72d6fae1e273b5322d508629221e11ea6f


[ROCm/clr commit: b35f5215b2]
2020-09-29 21:32:24 -04:00
Sarbojit Sarkar 1d5784202c SWDEV-253654 : Added invalid parameter checks
Change-Id: I8a2ae1ee6898f111aac1c68663a653cca410daec


[ROCm/clr commit: d4fa2e8c80]
2020-09-29 13:20:27 -04:00
Julia Jiang 8976ef0471 SWDEV-247518-fix HPC multi gpu test performance drop
Change-Id: I2f07d9ba183cf88b3845d8d61607a8a0462d015f


[ROCm/clr commit: 3d59e050db]
2020-09-29 12:04:40 -04:00
Sarbojit Sarkar 596fa95c9b SWDEV-252337: Fix for V100 compilation issue
Change-Id: Ib57ff3ac28f0a581f395f32181974e64eca6d858


[ROCm/clr commit: 7da8264b7c]
2020-09-25 21:55:22 -04:00
Julia Jiang 3ab02902f4 SWDEV-253250-update instruction for hip sample
Change-Id: Iebc2887a3687e6c565999f4faf1cd4cf893e24cd


[ROCm/clr commit: f93a2b03ad]
2020-09-25 13:51:19 -04:00
Aryan Salmanpour 58a6e2f0f2 fix a pagefault when wrong argument (extent) passed in hipMemset3D API
Change-Id: I779fc14ccd7c942d1ae0a938ebfd3c2e728ff761


[ROCm/clr commit: a680b514b3]
2020-09-25 10:57:37 -04:00
kjayapra-amd c15524b728 SWDEV-241896 - Remove extern support in ROCclr/HIP since compiler added Texture reference support.
Change-Id: I1b0a7377b803b4e2b94ffef6ffd91e376fdb2b2f


[ROCm/clr commit: 19acb0bfe5]
2020-09-24 14:28:16 -04:00
Rahul Garg b1851cdc96 Return hipMemoryTypeHost as memory type for hipHostRegistered pointer
Fixes SWDEV-253741
Change-Id: I42c2c9df00862157314d5767b6f175a0d2f28b47


[ROCm/clr commit: 2f3d60fc4a]
2020-09-24 12:27:32 -04:00
agodavar dc55fb39c0 SWDEV-249870 - Short-Term solution for Pre-Compiled Headers for Online Compilation
Change-Id: Iec989787e546ff2eb68c4b146dc540655698b569


[ROCm/clr commit: 3c9bbc335a]
2020-09-24 12:18:06 -04:00
Lakhan singh Thakur 3ef655ac27 [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


[ROCm/clr commit: eedf4c68dc]
2020-09-24 10:05:21 -04:00
kjayapra-amd 26a6b8b043 SWDEV-253349 - Add a SKIP state for hip directed tests when HIP_BRINGUP_SKIP macro is used.
Change-Id: If176cf775e568d4b32982127731223fe96a38f0d


[ROCm/clr commit: a363eeb4f4]
2020-09-23 16:46:21 -04:00
Sumanth Tumbalam Gooty 28e7ffcca6 [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


[ROCm/clr commit: 612bfc87f2]
2020-09-23 09:20:01 -04:00
Lakhan singh Thakur ff59dfbf67 [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


[ROCm/clr commit: 591905915a]
2020-09-22 23:49:30 -04:00
Aryan Salmanpour 0d577cdfd4 use only hip compiler to compile hip cooperative groups
SWDEV-252377

Change-Id: I6cf749dad2bf05c2e49fed495ab2833c574c2215


[ROCm/clr commit: c197183818]
2020-09-22 14:34:05 -04:00