2
0
Gráfico de cometimentos

5708 Cometimentos

Autor(a) SHA1 Mensagem Data
Tao Sang 10f4918d97 Remove unnecessary stuff from hip cmakefile
Remove the following from hip cmakefile,
1.find_package cmds of hsa-runtime64 and amd_comgr;
2.macros of USE_COMGR_LIBRARY and COMGR_DYN_DLL
because they have already been used in Rocclr cmakefile.
cmake mechanism will make hip cmakefile inherite them.

Change-Id: I03b527fc4135c79bb35cbbfe419211ec363cb067
2020-11-13 15:01:32 -05:00
Sarbojit Sarkar 25c8b41cb5 [SWDEV-259216] Minor test bug
Change-Id: Ib2ece421af88c99ded41514b6a2dc432b78be682
2020-11-13 02:23:45 -05:00
Sarbojit Sarkar c68a36fe14 [SWDEV-257048] fix for softhang in dtest
Change-Id: Ic77f5d9c13852c4e3da7afb41b1db7d43c5cbf75
2020-11-13 02:21:00 -05:00
agodavar 9ef681a618 SWDEV-249870: Generate Pre-Compiled Headers from includes in source repo for Online Compilation
Change-Id: I663f510603e983927f80f7944df4d039ba7bc0b0
2020-11-12 10:50:33 -05:00
jujiang f2d68da7c4 SWDEV-259096-update HIP documents
Change-Id: I78294ca55649634ef9eff5c4e38636cb17f5e640
2020-11-11 16:29:52 -05:00
Julia Jiang eacb30afcd SWDEV-249486-re-organize doxygen HIP API
Change-Id: I3d107de526e428ae16c6dffd97d9388bf54a6358
2020-11-11 13:31:56 -05:00
German Andryeyev d4e642203c Add an early exit if it's a null stream wait
Change-Id: I577f5da2f928bff172d64d511a60e08eda28c81d
2020-11-11 13:20:04 -05:00
Konstantin Zhuravlyov 73fb01cb3a SWDEV-198415 - Implement Target ID Proposal
Changes from Jatin Chaudhary, Tony Tye

Change-Id: I14904920ad2356ae2098cf827b83613089d33962
2020-11-10 13:31:43 -05:00
Tao Sang 272f89a966 Make hipMemset*Async* tests pass in static lib
3 hipMemset*Async* direct tests will crash in static lib because
some hsa objects are not initialized when hip apis call them.
The fix will make the hip apis called in main() so that hsa objects
have been initialized at that stage.

Change-Id: I41eb29b8c2588acac0cd3ae6d96b14fb1abd235a
2020-11-03 09:54:30 -05:00
Sourabh Betigeri b0664a0087 SWDEV-255694: Include attributes - hipFuncAttributePreferredSharedMemoryCarveout and hipFuncAttributeMaxDynamicSharedMemorySize
Change-Id: I3569859e6db0c59a10a76c8ea356d4bc0a0bb906
2020-11-02 19:39:39 -05:00
agodavar c7aa311537 Fix building of tests on nvidia GPU
Change-Id: I02b527ec4135c79bb35cbbfe419211ec363cb065
2020-11-02 09:42:28 -05:00
Tao Sang 6db4976759 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.Install rocclr when rocm is installed.
    6.Fix some original small bugs.

Revert "Revert "Make directed_test support static libs""
This reverts commit 0d1cf31eb1.

Change-Id: I918eeae94487e5e2ff5bfde083667ac65fb6e702
2020-10-26 12:39:58 -04:00
German Andryeyev ae8aec4834 Update documentation
Add managed memory section for the doxygen documentation.
No code changes.

Change-Id: I2e9db4ec13422159e265193916f0a3cdb721732d
2020-10-23 18:28:43 -04:00
Rahul Garg 9252b3a3d9 Fix performance tests for OSDB failures
SWDEV-257745- [ROCm CI][mainline] hiprocclrtests broken on OSDB - vg20 and mi100

Change-Id: I36b4ace7e8c2673809c4b0be569250e8f9b06da8
2020-10-23 00:48:08 +00:00
agodavar 8717a78bf7 cmake hip-rocclr as default build,change HIP_PLATFORM to amd|nvidia
Change-Id: I59d2e15b297b6ca2d5eee1a6dee642bdb01a3839
2020-10-21 07:26:14 -04:00
Sudheer Kumar f9d3e5a7be [dtest] Tests for loading hip apis dynamically
SWDEV-238517 for enhancing hip unit tests

Change-Id: I9b6ef41db2f02ee3679360d0fae709a404a0ea4f
2020-10-21 02:49:49 -04:00
Sourabh Betigeri b65314d168 SWDEV-251091: Added null checks and empty file check in hip_module and hip_platform
Change-Id: Iad99f996dcf90ffb86f62e79bf4cbd53b35b7e3b
2020-10-20 19:55:01 -04:00
Payam 4e96bfecd5 Cleaning lintian warning SWDEV-247996 Part2
Change-Id: I40eb29b8c2588acac0cd3ae6d96b14fb1abd2350
2020-10-20 19:27:38 -04:00
Aaron En Ye Shi 01bd165507 Fix header for OpenMP AMDGCN support
Add ifndef for __OPENMP_AMDGCN__ target, which shares
these header files with HIP.

Change-Id: I720693cfbcfb7836cd2f361d48530fb55ee3557a
2020-10-20 14:04:48 -04:00
kjayapra-amd c18a791c80 SWDEV-250005 - Fixing error code propagation to HIP outer layer.
Change-Id: I0c0e87dbace0b1182f24411200abdfd9cab3f865
2020-10-20 09:43:57 -04:00
Sarbojit Sarkar a73d1a1fe0 SWDEV-256325 : Fix for hipMemset2D crash
Change-Id: I1f434602fecd4fb935d2bc72f2c72d6a2d4c45fe
2020-10-20 02:54:29 -04:00
Rahul Garg 3979d063a1 Bump version to 4.0
Change-Id: Ia8c3b21ccd58f07c95aa3030bc787144f934f80e
2020-10-19 21:00:13 -04:00
Aaron En Ye Shi bd9ed9ad3d Fix header invalid sqrt fwd decl and ifdef
The __ocml_sqrt_* functions only accept a single arg,
not two args. Also, change ifdef for if because the flag
__HCC_OR_HIP_CLANG__ is always defined.

Change-Id: Id9dc4eaf0f25df1df27a1bf643cb545ac23653f8
2020-10-19 18:01:14 +00:00
Rahul Garg 4b7c8f5fc1 Fix PCI bus domain ID query
SWDEV-256338

Change-Id: I5db361bd2899a5bf761ecf05ecd4635f9e3dce1d
2020-10-19 12:02:50 -04:00
Sourabh Betigeri 7513454a28 SWDEV-254134: Added new perf test - Vector Dot product in performance/compute
Change-Id: Ic2900fe9a1b6b197cdc8c2dd0f93723a8f73f14c
2020-10-16 13:07:13 -04:00
Rahul Garg cc1101f97a Fix maxTexture1D query
Needed by SWDEV-254068

Change-Id: Ib43a3e5e96d3882af354208063e5502673c0f35a
2020-10-14 17:32:04 -04:00
Julia Jiang 5a174daa09 SWDEV-249486-Update HIP doxygen
Change-Id: Id32772b8f4d495e0f1bd3cb5cd1ec211a06298c3
2020-10-14 13:59:58 -04:00
Yaxun (Sam) Liu 4c4fff6b51 Fix test hipDynamicShared
This test does not work if block size is greater than wave size
since it relies on lock-step execution of the kernel in the block.
If there are more than waves in the block, the threads in the block
miss synchronization since one wave may finish before another wave.

Due to this bug, the test fails on GFX10 wave32 mode.

This patch fixes that so that it works for block size greater than
wave size.

Change-Id: Ie0097066081df36cb6fe025a71d0ee5a83ec00a2
2020-10-14 10:15:44 -04:00
Sarbojit Sarkar 40f27ec83a SWDEV-255975: fix for gcc + hip_fp16.h compilation error
Change-Id: Ia152bad4af71a5b53a16e2f9fd9aeeacc61b39ac
2020-10-14 06:57:25 -04:00
Sarbojit Sarkar 3b8b31a61c Added sample with __gfx*__ macro used
Change-Id: I80a474947ea1b755082dad5329d1aff3ee78840c
2020-10-14 06:56:39 -04:00
agodavar 4018464960 SWDEV-249870: Short-Term solution for Pre-Compiled Headers for Online Compilation - Fix static build
Change-Id: Ib608e73dbffa2d803599cba5ba842cd5a2a2ba9d
2020-10-14 00:37:46 -04:00
German Andryeyev 15ba5611ba Report managed memory capabilities
Change-Id: I241a42e26ee49fb47dcb3ba87c4bd8fb691dffdf
2020-10-13 16:09:43 -04:00
Rahul Garg 85715bc20f Clean up unused options
Fixes SWDEV-253092

Change-Id: Ic820c4d7bec1130978b47094f3ad9764e40e6a1f
2020-10-13 12:19:20 -04:00
Aryan Salmanpour 89964dbbd4 Fix a seg fault when unallocated mem handle passed to hipIpcOpenMemHandle API
also validate the flag argument passed to hipIpcOpenMemHandle API and return
error if it is not equal to "hipIpcMemLazyEnablePeerAccess" (defined to 0)
and it is the only supported flag currenlty for this API.

SWDEV-253462

Change-Id: Ie1c8b79c680a29dc72bf262cf53ae5e011fb1247
2020-10-13 11:14:41 -04:00
Lakhan singh Thakur 04b773471b [dtest] Adding Test case for hipFuncSetSharedMemConfig() and hipFuncSetAttribute()
SWDEV-251504 - QA task for validation

Change-Id: I11ed98f648352cb32161c41290516c77231236bc
2020-10-13 11:11:00 -04:00
Rupam Chetia 4f48154f46 [dtest] hipModuleLoad and related API tests
APIs: hipModuleLoad, hipModuleLoadData and hipModuleLoadDataEx,
      hipModuleGetGlobal(), hipModuleGetFunction
Functional and negative tests
Repeated call to ModuleLoadXX/ModuleUnloadXX
Few tests are disabled now, will be enabled when functional

SWDEV-238517 for enhancing hip unit tests

Change-Id: I65c12027e32db80213468fdee1c5cc1aa3e60bfd
2020-10-13 11:10:11 -04:00
Julia Jiang c144b57d54 SWDEV-249487-remove two HCC related APIs
Change-Id: Icf90ece0808643e0c5f0cc00b6644d5171b553d8
2020-10-13 11:08:37 -04:00
agodavar e65bbb0329 SWDEV-255853: CUDA device P2P attributes
Change-Id: I7deffd04101b565f68a72a179f9faeaa22cab97d
2020-10-13 05:32:29 -04:00
agodavar fae443cb36 SWDEV-254909:Support for missing texture/array cuda driver types
Change-Id: I9c769f6335ec3e7feacaa8929719c666bff91934
2020-10-13 05:30:31 -04:00
Freddy Paul 5a46d80682 HIP:Break dependency to rocm-dev package
Check for rocm_agent_enumerator instead of rocminfo or
.info/version.

Change-Id: I1718bd4f70b3e527ea3afe19c1a685ab7ed70808
2020-10-12 17:53:53 -04:00
agodavar 7d67573a4f SWDEV-254185 - Added support to pass include headers to hipRTC
Change-Id: Ia19e6806a476d3c6ecd3e9a89c3ed72953a4900c
2020-10-12 06:04:14 -04:00
Tao Sang 0d1cf31eb1 Revert "Make directed_test support static libs"
This reverts commit 36c5679efc.

Reason for revert: <INSERT REASONING HERE>

Change-Id: Ib2d1084ea21461f70f96f95c6025a08f88288357
2020-10-12 00:01:13 -04:00
Sameer Sahasrabuddhe 160dfb5a1f 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
2020-10-10 01:03:04 -04:00
Yaxun (Sam) Liu 147f064d31 Disable wave64 support on GFX10 for HIP
Change-Id: Ie3d4fe91516167ea26ce704689b6b6f1951a7521
2020-10-09 17:02:56 -04:00
Tao Sang 36c5679efc 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
2020-10-08 22:46:58 -04:00
Jason Tang f2c2fd3d09 Add hipStreamSynchronize to hipModuleLoadDataMultThreadOnMultGPU test
hipStreamDestroy() by definition doesn't guarantee waiting for all stream operations.

Change-Id: Ibfd21c48d71741ebcbcb9898c8b5ac235bdc570b
2020-10-08 11:06:39 -04:00
Payam 95bef523fe Cleaning lintian warning SWDEV-247996 Part1
Change-Id: Ie024912b65125c3e14ecc278ac12e07912df6354
2020-10-08 05:44:58 -04:00
German Andryeyev 4ee6d78763 Use more managed memory interfaces
Add extra API calls for managed memory: hipMemAdvise, hipMemPrefetchAsync,
hipMemRangeGetAttribute

Change-Id: Ifb09744acdf7582d278453707373c89c30e3ed03
2020-10-07 16:45:25 -04:00
sumanthtg 00d46218b7 [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
2020-10-07 13:20:12 -04:00
sumanthtg 4eb65d58dd [dtest] Additional tests for hipOccupancyMax APIs
Additional tests for following APIs
- hipOccupancyMaxActiveBlocksPerMultiprocessor
- hipOccupancyMaxPotentialBlockSize

SWDEV-238517 for enhancing hip unit tests

Change-Id: Ib9441c1366f46a082e10eb1a572bc7d8ebe1ee37
2020-10-07 13:19:06 -04:00