Граф коммитов

4874 Коммитов

Автор SHA1 Сообщение Дата
Aryan Salmanpour bb8828bf7b Fix a warning with cooperative groups header
SWDEV-252413

Change-Id: Ia098464b670f26416b79cc67805b8accb6bec903


[ROCm/hip commit: ddceeac8eb]
2020-09-18 13:38:47 -04:00
Satyanvesh Dittakavi 89524aad2c Print size_t variables with %zu
Change-Id: I02bb073b07e9efd03dea2b76b6ba1bd2f552bcaa
Total Memory is not being printed correctly with %u.
%zu represents size_t variables appropriately.


[ROCm/hip commit: cede497cb2]
2020-09-18 11:55:41 -04:00
Lakhan singh Thakur 50f20a494d [dtest] Cooperative Groups related tests
Converted tests from below git to hipdirected_tests
http://gitlab1.amd.com/jgreatho/cuda_cooperative_groups_test
Modified to cover multi-GPUs
Disabled tests for cuda because of some header file issues

SWDEV-238517 for enhancing hip unit tests

Change-Id: If35fd710e8ab61debcf66bca5b6503539c567ec1


[ROCm/hip commit: e955144aa3]
2020-09-18 11:40:16 -04:00
Tao Sang be63180abe Make samples support cmake
Only cmake can support static lib of hip rt.
Thus samples will support static lib of hip
rt when this is done.

Change-Id: I70e8d06e85084369a035b42c5d1d56287c874ac9


[ROCm/hip commit: 8f72a6993f]
2020-09-18 07:37:02 -04:00
mkumarmi 7f4fd6e62e [dtest] Disable few tests on NVCC platform
Few of the tests are being validated in nvcc platform.  Till then
these tests are disabled.

SWDEV-238517 for enhancing hip unit tests

Change-Id: I1acbfe90c6ea39f3de676e98f0e3c33cbac97888


[ROCm/hip commit: 5bf2a70382]
2020-09-18 04:34:00 -04:00
kjayapra-amd ec47e5a7d4 SWDEV-241902 - Changes to pass file descriptor and offset to load code object.
Change-Id: I96add27f4fde1b5ee5501e206b7e85ab77e87dfc


[ROCm/hip commit: 89e5e8b90c]
2020-09-15 07:54:28 -04:00
Rahul Garg 2bdb08bbe7 Reinsert __gnu_h2f_ieee and __gnu_f2h_ieee.
Fixes SWDEV-251676

Reverts Ide24d245d851e20961020323e52f33322a33fff9 and adds
__attribute__((weak)) to __gnu_h2f_ieee and __gnu_f2h_ieee.

Change-Id: If4f9e2f867b56a3f0121a907a49ae4032220d9af


[ROCm/hip commit: 5241c76a9d]
2020-09-15 01:39:14 -04:00
kjayapra-amd 0189887c71 SWDEV-251884 - Add Coop Launch Dev Property Checks in Co-operative Groups test cases.
Change-Id: I7b54a559d8abe0d5d5c77e48868b1332477a39f8


[ROCm/hip commit: e71067a7ec]
2020-09-14 17:10:39 -04:00
kjayapra-amd ba88ed195f SWDEV-251941 - Adding gfx1030, gfx1031 support to mainline.
Change-Id: Ifbe0d72646f5f00c7b8e16338587fc564a314b92


[ROCm/hip commit: 9d9602aca5]
2020-09-14 17:10:17 -04:00
Sarbojit Sarkar 5d64e17af6 Updated hip_porting_guide.md
Change-Id: Iaf32033597513aa2cbfde267487af35317ac67fe


[ROCm/hip commit: b1f79c9a33]
2020-09-14 00:30:51 -04:00
Julia Jiang bf74cda079 SWDEV-249486-Update Doxygen configuration file to link correct documents
Change-Id: I2bbe2a0dedec2d182bd3108c3d5af04f3d8beed8


[ROCm/hip commit: 66927332f5]
2020-09-11 16:45:07 -04:00
kjayapra-amd da79b0a5d2 SWDEV-240800 - Adding dtest for hipDeviceGetP2PAttribute.
Change-Id: Icf1dc56c98247de43c638d9fdc16de045d2a1da9


[ROCm/hip commit: 637e8f966c]
2020-09-11 14:25:11 -04:00
Rahul Garg 910a818188 grid size optimization
Change-Id: I68b197548b961e1c0aa63119eecc8d9a25350cf2


[ROCm/hip commit: 188278b38a]
2020-09-10 15:10:55 -04:00
Sarbojit Sarkar 00632b266c Fix for hipPointerGetAttributes [github#2137]
Change-Id: I5295575638ecc4d3b7129552a9c26c6f6a7195fc


[ROCm/hip commit: 5c7b7d1dd2]
2020-09-10 10:51:30 -04:00
agodavar d9eef29787 SWDEV-249870 - Short-Term solution for Pre-Compiled Headers for Online Compilation
Change-Id: Ibcb365ce2ff27c4c2379609964078da42e1226b1


[ROCm/hip commit: 9e2fa6e215]
2020-09-09 13:44:13 -04:00
Siu Chi Chan 54247e053b fix no matching push_macro warmnings
Change-Id: I352fe1170cfc9e8de5307536a21c86f0b483c68e


[ROCm/hip commit: bf0d8f37e4]
2020-09-09 11:41:07 -04:00
kjayapra-amd 7970890e4b SWDEV-240800 - P2P device attributes support
Change-Id: Ia32b87ffea17e0d98b69a07f2633ba14e7637b8a


[ROCm/hip commit: 1f8543560f]
2020-09-03 09:41:05 -04:00
Rahul Garg 91b45333cb Fix dependency on rocm-dkms pkg
SWDEV-249463- hipcc can't find the rocm_agent_enumerator

Change-Id: I768a0d09753047508734d8360eb3d154edc0b0ef


[ROCm/hip commit: df1dc87d0f]
2020-09-03 03:30:59 -04:00
Satyanvesh Dittakavi 88c3a16a69 SWDEV-248293 - Fix elapsedTime
Fixes the elapsed time for the scenarios where HIP API takes one of the start/stop events
and another one is recorded using hipEventRecord.


Change-Id: I51831b2651fc8e7207ff0e3fcc6dc7c1b4239fa8


[ROCm/hip commit: 08cf695e1f]
2020-09-02 03:22:47 -04:00
agodavar a6accd4db6 SWDEV-246142: Improve performance for sync with multiple streams
Change-Id: Ifc625c4c1311ac235b08ea705a3df216d47b2c5e


[ROCm/hip commit: 76824a7f04]
2020-09-02 00:56:46 -04:00
Saleel Kudchadker 7c60cf0a5b Fix hipPrintf* tests
The test needs to check dup2 syscall status and not the
errno val

Change-Id: Ic88eb2047b839adbc9e12965b098d8960cd7e2b8


[ROCm/hip commit: 7720651f2d]
2020-09-01 15:00:49 -04:00
Tao Sang f985a8d247 Replace private libelf with elfio
Change-Id: I59ae33f7cc55e73f6519af14be91dd9863b03af3


[ROCm/hip commit: 4e1344de0f]
2020-09-01 10:29:11 -04:00
Rahul Garg d0229930f9 Revert "[dtest] Additional tests for Memcpy"
This reverts commit fc61d76630.

Reason for revert: All the PSDBs on the CI are failing with the below error and its been root caused to this commit:
......................................................................................... Passed 0.59 sec 99% tests passed, 1 tests
failed out of 211 Total Test time (real) = 287.02 sec The following tests FAILED: 139 - directed_tests/runtimeApi/memory/hipMemcpyNegativeMThrdMSize_Negative_tests.tst
(Child aborted) Errors while running CTest Restoring clocks to: auto

Change-Id: I4ea0e14ba5f92cd61677f4a3b9482fea00902310


[ROCm/hip commit: 280d300320]
2020-09-01 00:48:20 -04:00
Jatin Chaudhary bb96f35660 Adding dim3 conversion operator to __hip_builtin_threadIdx_t
Change-Id: Ib7f9e45872ec6d48c0e5b7fc93ccecaafaeac754


[ROCm/hip commit: fef8df6e2e]
2020-08-31 21:30:14 -04:00
kjayapra-amd 43e91c1e7b SWDEV-245296 - Adding performance test for hipModuleLoad/hipModuleGetFunction
Change-Id: I4b66d33dc58430e88be4b9b39bc4037e4e53d11e


[ROCm/hip commit: cec4f3b433]
2020-08-31 13:43:58 -04:00
Rahul Garg ad72b42e36 Return error when mismatch in copy kind and ptrs
Change-Id: I70e4d06e850843697035b42c5d1d56287c874ac8


[ROCm/hip commit: 519ef3f22e]
2020-08-27 20:53:48 -04:00
Vladislav Sytchenko 02913e98a3 Fix memory leak
getLastQueuedCommand(true) will implictly retain the last command, hence if we're not putting it in the waitlist, we should release it.

Change-Id: I1ad4ddcdf1df5237b83e1ea2447eb39a59f7dc3a


[ROCm/hip commit: 61b84e246c]
2020-08-26 12:45:18 -04:00
Aryan Salmanpour 088512e3f6 [HipPerf] modifiy and move hipPerfMemcpy test to the new location for perf tests
SWDEV-245290

Change-Id: I84f03a3019fce48aab63dd4cc232ea3539a1af79


[ROCm/hip commit: 1c966637a4]
2020-08-25 16:52:14 -04:00
mshivama 9204746c65 Support public apis for cooperative group types.
Change-Id: I01346afde485e82c34b7868b9241b34c542d0cf9


[ROCm/hip commit: 15aff89ba1]
2020-08-25 10:50:38 +05:30
Rahul Garg 8a5b10a216 Bump version to 3.9
Change-Id: I5dfc997336fac42f3b6b0998a4bb212462de38f9


[ROCm/hip commit: 2380cf7805]
2020-08-24 21:52:22 -04:00
kjayapra-amd 16b52c4a62 SWDEV-249499 - Add message to Guarantee assert code in hip runtime.
Change-Id: I1850463675bbc3e6ff5e3cef8211b1fd40e55f96


[ROCm/hip commit: 9c75797d9f]
2020-08-24 17:35:39 -04:00
Yaxun (Sam) Liu 4fcbffd307 Fix hipcc for extracing clang version
On teamcity clang --version returns something like

clang version 12.0.0
Target: x86_64-unknown-linux-gnu

currently hipcc does not handle it correctly since [^ ] causes new line and Targe:
matched. \S will make sure only version string matched.

Change-Id: I3659d6daf89b709d2b001e6b8024d69d8b79efc0


[ROCm/hip commit: d537bb3859]
2020-08-21 18:21:46 -04:00
Todd tiantuo Li d42822325f SWDEV-240803 - add hipFuncSetSharedMemConfig
Change-Id: I160b04677b3e7b99b3981ae7ecc84a0e3811d5e8


[ROCm/hip commit: 99eb486937]
2020-08-20 18:18:24 -04:00
Lakhan singh Thakur fc61d76630 [dtest] Additional tests for Memcpy
APIs tested: hipMemcpy, hipMemcpyAsync, hipMemcpyHtoD, hipMemcpyHtoDAsync
             hipMemcpyDtoH, hipMemcpyDtoHAsync, hipMemcpyDtoD,
             hipMemcpyDtoDAsync

-Scenario-1:: The aim of this test case is to cover all the negative test cases
              for 8 hipMemcpy apis
-Scenario-2:: This test launches NUM_THREADS threads. Each thread in turn tests
              the working of 8 hipmemcpy apis
-Scenario-3:: This test case verifies the working of Memcpy apis for range of
              Memory sizes from smallest one unit transfer to 1GB.

SWDEV-238517 for enhancing hip unit tests

Change-Id: Iace19cc54e865fae8450448d6f37abed88597f19


[ROCm/hip commit: 858b7e027e]
2020-08-20 16:41:57 -04:00
Sudheer Kumar cfc658478b [dtest] Enhanced tests for hipSetDevice and hipGetDevice
SWDEV-238517 for enhancing hip unit tests

Change-Id: I4fe169c560ce2e1fb471df67f03263903b12463b


[ROCm/hip commit: f648d2f2f5]
2020-08-20 13:52:05 -04:00
Sourabh Betigeri 3c94c833ee SWDEV-246104: Added new performance test to verify stream concurrency
Change-Id: Ieceaafd4d404b137936eb8aceecff27bbba42026


[ROCm/hip commit: cb2026c945]
2020-08-20 13:42:55 -04:00
Aryan Salmanpour 2917131b74 [HipPerf] add a test for measuring create/copy/destroy for hip streams
SWDEV-245290/SWDEV-247767

Change-Id: Id52e3d2f7afee52763da107eb5ed04627942d9f0


[ROCm/hip commit: aafc12e7c1]
2020-08-20 13:28:36 -04:00
Todd tiantuo Li ba5b0b38c6 move hipFuncSetCacheConfig from hip_device to hip_module
Change-Id: If5a930e1210e76531f5ba9a0e5f5ec98ad473a19


[ROCm/hip commit: efcb882e19]
2020-08-17 17:39:01 -04:00
Aryan Salmanpour e3f344ba99 SWDEV-248057 - fix the calculation of allGridSize used in multi_grid_group() API
Change-Id: Ib470094e28dcacaa4769dc5c7ab08924f5b7fa41


[ROCm/hip commit: 4f400bc5e9]
2020-08-17 12:52:40 -04:00
Jatin Chaudhary 788f07b626 Adding Anyorder flag to HIP
Change-Id: Ie20931541b3febe23fa9ac36ebc0c90de75a5f0a


[ROCm/hip commit: 1340b3f07f]
2020-08-17 08:46:52 -04:00
Rahul Garg dd5cdce6d2 Fix hipDispatchEnqueueRateMT sample
Change-Id: I7ade0dcf8b32ac90a311022d12339740b2b3df44


[ROCm/hip commit: dd40abe96c]
2020-08-14 18:56:39 -04:00
Todd tiantuo Li 92157f4482 SWDEV-240803 - add hipFuncSetAttribute and hipFuncAttribute
Change-Id: I3f4d67b19d89fd348fa5b884af4a2542ee4aba60


[ROCm/hip commit: 9dfe15a843]
2020-08-14 17:39:29 -04:00
kjayapra-amd 5d34185549 SWDEV-237658 - Do not attach events to user invisible Marker.
Change-Id: I3a74fd2614d6e2e1d51543471bbd5ae51a713a47


[ROCm/hip commit: 6f8909be34]
2020-08-14 10:55:34 -04:00
Freddy Paul 0f495a009a Enable developers to build hip without CMAKE_PREFIX_PATH
With recent changes in ROCclr to take HSA cmake target it require
HIP to have CMAKE_PREFIX_PATH added for install location for HSA,
amd_comgr,llvm.

User can provide CMAKE_PREFIX_PATH if above
packages are built/installed at custom location as:
cmake -DCMAKE_PREFIX_PATH="<path_hsa> <path_amd_comgr> <path_llvm>"

For default ROCm installation adding a default path will help.

Change-Id: Iefa443dc198da76b57422a641c9821c63cde4922


[ROCm/hip commit: 6e50c0f755]
2020-08-13 23:13:40 -04:00
Aryan Salmanpour 249cb857ed [HipPerf] relocating/renaming some hip perf tests
Change-Id: Ie85d242cd68cd14a858e07ed27875a5196014688


[ROCm/hip commit: 0d0efcdbf4]
2020-08-13 17:28:11 -04:00
Aryan Salmanpour 3895911e4d [HipPerf] report performance based on wall time only for hipPerfDevMemReadSpeed/hipPerfDevMemWriteSpeed
Change-Id: I1fda2ec76da6fad6852d328e0a3fc39e28af57bb


[ROCm/hip commit: a8e7816726]
2020-08-13 14:23:58 -04:00
Jason Tang cba6c9a60f SWDEV-232197 - Remove refering to gfxipVersion_
Change-Id: I91b6b972e26b18dabf6deda5a142bff491c8bb45


[ROCm/hip commit: e2169ce6d0]
2020-08-12 16:34:18 -04:00
German Andryeyev 9e30284904 Allow prefetch on the null stream
Change-Id: I87e950460361fab65ab140988fc2288bcb194f08


[ROCm/hip commit: 505877acea]
2020-08-12 13:07:43 -04:00
Rahul Garg da32b4f5b6 Return error from hipMallocManaged for size =0
Change-Id: Ida0cecf05e1df731176d41e59422d1e606cc9bd9


[ROCm/hip commit: d620a25b64]
2020-08-10 18:25:31 +00:00
Vlad Sytchenko 003e50f6cb Don't align 2D image buffer size
Cuda allows creating 2D textures from memory with unaligned size.
Aligning it will cause us to overshoot the size of the underlying
allocation.

Change-Id: Ia20dec2105e36ca4a8448c9c6299d0001b388d25


[ROCm/hip commit: 844dab3b22]
2020-08-09 15:53:52 -04:00