커밋 그래프

869 커밋

작성자 SHA1 메시지 날짜
Aryan Salmanpour 72a611f9e3 [dtest] add a test for hipExtStreamCreateWithCUMask API
Change-Id: Ib567e559c5ab7d04ac5c300fd7e15eedfc4fb6e6


[ROCm/hip commit: 9b6228f6c9]
2020-05-26 18:15:09 -04:00
Mahesha Shivamallappa 5d530df13d Add support for cooperative group type - thread_block
Change-Id: If3770b6d6718a638b70f527ae2533d9ef3267ff4


[ROCm/hip commit: 01dae52d64]
2020-05-22 23:08:42 -04:00
Vlad Sytchenko b91cc2fbfb Reenable texture reference tests
Change-Id: I77024476cff77951d61dc48f7e30094d6b47266c


[ROCm/hip commit: 81ba0fcfd9]
2020-05-22 14:13:50 -04:00
German Andryeyev 20e64e1450 Add a test case for async double memset
Change-Id: I8a1df610c8d3d942651f258e7812e8697067c347


[ROCm/hip commit: 4503d44e12]
2020-05-20 12:52:29 -04:00
agodavar e5c6555eee Fix hipMemset for unaligned ptr, correct offset required by ROCclr per aligment and testcase to validate unaligned ptr
Change-Id: Ib1a0f9d1556d09cf72a12a90cad2e27c6d9c6a1c


[ROCm/hip commit: 458a966aa1]
2020-05-16 02:38:14 -04:00
German Andryeyev 9b69ab8053 Merge "Correct mgpu coop launch test" into amd-master-next
[ROCm/hip commit: d461c82dc7]
2020-05-13 16:20:24 -04:00
German Andryeyev 80bd9632ad Correct mgpu coop launch test
When the original size is devided accross all GPUs rounding can
occur, causing incorrect validation. Readjust the final value
for comparison to the new size accordingly.

Change-Id: I9b42149e33dfcb328de7419e546a0202a69a8610


[ROCm/hip commit: 20f0e36041]
2020-05-13 14:39:11 -04:00
Matt Arsenault 3a07d0e785 Remove some asm declarations for intrinsics
This technique should never be used, and only accessed through
__builtins.

There's currently no builtin for groupstaticsize. I left ds_swizzle
since for some reason it switches to the builtin based on __HCC__ or
not.

Change-Id: If1e1394221dba83ea4add6db5e94d6b715552044


[ROCm/hip commit: d2dd307c7d]
2020-05-11 15:20:58 -04:00
Tao Sang afbd11eb66 Support performance tests
Support performance tests while direct tests commands keep unchanged.
To build performance tests, run "make build_perf".
To run all performance testis, run "make perf".
To run specific tests, for example, run
/usr/bin/ctest -C performance -R performance_tests/perfDispatch --verbose
To run individual test, for example, run
performance_tests/memory/hipPerfMemMallocCpyFree

Change-Id: I168c1b9ef1ec21b392d48648d0c71e8fbd37d57b


[ROCm/hip commit: 6e972dd3bb]
2020-05-06 14:06:07 -04:00
Payam 0c8b343931 name change vdi to rocclr
Change-Id: I06d198bbb4a499e153b290b73a92afed3553b252


[ROCm/hip commit: c5f76c3de3]
2020-05-06 09:14:30 -04:00
agodavar 41a1bb6733 find_package(hip) changes for clang
Change-Id: I9dc1be1dd5f9424e26ebcd2961207e1c4467550f


[ROCm/hip commit: 1468982f8a]
2020-05-01 20:48:32 +00:00
root 2061d19165 Merge master into amd-master-next
Change-Id: I3fc1dc0c860d627053537581e75561e8a7efe327


[ROCm/hip commit: 2689246de6]
2020-04-26 22:19:37 +00:00
Yaxun (Sam) Liu f79898e90e Enable template max and min for HIP-Clang (#2028)
It was for HCC only. HIP-Clang also needs it for __fp16 since AMDMIGraphX uses it.

Change-Id: Id49322b7b89ef799accdf6b47627a6fce51d1ab5

[ROCm/hip commit: 808dae6813]
2020-04-24 12:30:28 -07:00
Yaxun Liu 10cfc55ed3 Merge "Enable template max and min for HIP-Clang" into amd-master-next
[ROCm/hip commit: 8cb04db89e]
2020-04-24 11:44:49 -04:00
Yaxun (Sam) Liu 6f1a8d4e77 Enable template max and min for HIP-Clang
This change is required by AMDMIGraphX.

It was for HCC only. HIP-Clang also needs it for __fp16 since AMDMIGraphX uses it.

Change-Id: Id49322b7b89ef799accdf6b47627a6fce51d1ab5


[ROCm/hip commit: 4143d81618]
2020-04-24 09:51:17 -04:00
Tao Sang f94a1bd16d Add Performance/memory/hipPerfMemMallocCpyFree
Change-Id: Id1ac415f85028da3e9517c2226764bcb4acec1b1


[ROCm/hip commit: e130c3ba4f]
2020-04-23 23:49:56 -04:00
Maneesh Gupta 8e137a6ec1 Merge in the rocclr based hip runtime (#2032)
* Merge master-next changes in master (include vdi development in master branch)



[ROCm/hip commit: a0b5dfd625]
2020-04-23 09:12:06 -07:00
Tao Sang 7142f1c5c2 Merge "support hipLaunchParm test with static lib of hip-vdi rt" into amd-master-next
[ROCm/hip commit: 5fee28ce03]
2020-04-21 15:54:46 -04:00
Tao Sang 77190ec979 Add perfDispatch tests into hip direct_tests
Port perfDispatch tests from OpenCL into hip direct_tests

Change-Id: I9f8362636e329d2d0a434c4f012ccc46a524c746


[ROCm/hip commit: daf32606db]
2020-04-21 14:00:27 -04:00
Tao Sang 02c3baa938 support hipLaunchParm test with static lib of hip-vdi rt
Let hipMalloc() be called in main() so that global variable can be initialized.

Change-Id: I9aa1f0a0bb4fa0825d10af0b58c843e7b928e9a3


[ROCm/hip commit: de4c173c6e]
2020-04-21 13:55:42 -04:00
Michael LIAO c11c159905 [vdi] Refactor texture/surface reference support.
Change-Id: I8014d82aae7139ef5f95e4b50c4fc6da200dbc9d


[ROCm/hip commit: 16d9fe5e37]
2020-04-21 11:56:48 -04:00
Jeff Daily e428d45eb2 add IPC event support (#1996)
[ROCm/hip commit: ef596cd088]
2020-04-17 10:31:22 +05:30
Yaxun (Sam) Liu 3207f06462 Disable device side malloc (#2009)
* Disable device side malloc

Currently device side malloc is not working and takes excessive
device memory.

Disable it for now until a working malloc is implemented.

Change-Id: I1ad908c1c53a83752383b4be96688a848642c699

[ROCm/hip commit: 8d83e95457]
2020-04-14 16:07:14 +05:30
Yaxun (Sam) Liu e83752424d Fix MIOpen build failure
This is charrypick of b5a50ec9cf
and https://github.com/ROCm-Developer-Tools/HIP/pull/2009

Fix cmake config file

Removed cmake target files under packaging directory.

Merged cmake config .in files for HIP-Clang and HCC as one.

Use cmake generated target files in both install and packaging.

This makes cmake config file consistent for make install and
make package.

Let device side malloc/free return nullptr and trap

Change-Id: I448f3ea2d4934648089bad371debc203f895cba6


[ROCm/hip commit: 88304c15e6]
2020-04-13 23:01:31 -04:00
Maneesh Gupta 58cddfe335 Merge "Merge branch 'amd-master' into amd-master-next" into amd-master-next
[ROCm/hip commit: 21f1e6d5b8]
2020-04-10 01:11:03 -04:00
Vladislav Sytchenko f3040d7241 Disable all texture tests for VDI
Latest llvm already includes the texture/surface rework, but appropriate runtime changes have not been submitted.

Disable all texture related tests until http://gerrit-git.amd.com/c/compute/ec/hip/+/342147 is submitted.

Change-Id: I359c2eac6becdd3ca5110f2140679bd29d8ae54b


[ROCm/hip commit: de67236a27]
2020-04-09 14:02:40 -04:00
Maneesh Gupta 4e1f6f2a0e Merge branch 'amd-master' into amd-master-next
Change-Id: I3094c15008093f2072bcd38aca4ea90aeae2d97b


[ROCm/hip commit: 2af31479e2]
2020-04-09 06:31:00 -04:00
Sameer Sahasrabuddhe df03380378 printf test: loop with divergent exit condition
Change-Id: I1071e4a240a280332bde669701c72228b9dea2df


[ROCm/hip commit: 1d464f391e]
2020-04-09 10:20:11 +05:30
Rahul Garg 003d776e72 Rename hipDrvOccupancy to hipModuleOccupancy and match CUDA syntax (#1943)
[ROCm/hip commit: ba8a556ea9]
2020-04-07 14:02:52 +05:30
German Andryeyev 1c431297f1 Merge "SWDEV-184709 - support hipLaunchCooperativeKernel()" into amd-master-next
[ROCm/hip commit: b72ec19c0e]
2020-04-06 11:45:34 -04:00
Sarbojit2019 e10e59a8c0 hipEventElapsedTime should respect device (#1992)
Fixes SWDEV-228636.
Also added a unit test to verify this.

[ROCm/hip commit: b80a2c3966]
2020-04-06 15:38:25 +05:30
ansurya f59ed79983 Initial support for bfloat16 (#1980)
[ROCm/hip commit: 770e76e752]
2020-04-06 15:35:43 +05:30
Sameer Sahasrabuddhe 49184503f8 SWDEV-227201: Introduce tests for printf on hostcall
Tests that check POSIX specifiers with a single thread:
 - hipPrintfSpecifiers.cpp     : all conversion specifiers
 - hipPrintfFlags.cpp          : common flags that modify conversions
 - hipPrintfAltForms.cpp       : alternate forms ('#')
 - hipPrintfStar.cpp           : additional arguments ('*')
 - hipPrintfWidthPrecision.cpp : floating point details

Tests that check functionality on top of hostcall
 - hipPrintfBasic.cpp       : divergent calls, series of calls, return value, etc
 - hipPrintfManyWaves.cpp   : many waves printing together
 - hipPrintfManyDevices.cpp : many waves on many devices

Change-Id: I35e069f4c542f896999239996dc89eda0faad7b8


[ROCm/hip commit: db3e17d552]
2020-04-06 00:49:34 -04:00
German Andryeyev 97926390dc SWDEV-184709 - support hipLaunchCooperativeKernel()
- Enable cooperative tests for single and multiple devices

Change-Id: I54b6713f578b6b5e670f117b17469c0091028c99


[ROCm/hip commit: 0d69b79622]
2020-04-02 12:55:05 -04:00
ansurya 1344399fa2 tex1Dfetch behaviour for different address mode and filter mode (#1772)
Fixes github issue: #1754

- When ResourceDesc::resType is hipResourceTypeLinear ignore address mode and filter mode.
- When textureDesc::normalizedCoords is set to zero, AddressModeWrap and AddressModeMirror won't be supported and will be switched to AddressModeClamp.

[ROCm/hip commit: 50ef250a3b]
2020-04-01 12:10:17 +05:30
agodavar d7db609b92 Update Enable/Disable peers to match cuda behaviour
Change-Id: I67194ccf77a0019368579ff7d95b7790fcf228f3


[ROCm/hip commit: bdb3a4b393]
2020-03-30 12:49:16 -04:00
Tao Sang aa94d9c654 Merge "Support hipFuncGetAttributes with hip-clang+Hcc RT" into amd-master-next
[ROCm/hip commit: af7d131749]
2020-03-27 14:36:41 -04:00
satyanveshd 3eea799a53 [dtests] Added few Negative tests (#1735)
[ROCm/hip commit: 351d39e6aa]
2020-03-27 14:10:12 +05:30
Sarbojit2019 1909e436cf Fix few memory leaks in HIP (#1969)
[ROCm/hip commit: f1b028b93e]
2020-03-27 14:08:30 +05:30
Tao Sang c20e13d1f0 Support hipFuncGetAttributes with hip-clang+Hcc RT
Fix issues of missing kernel function symbols and missing argument list via
using __hipRegister* functions.
Then the following tests can pass,
directed_tests/runtimeApi/module/hipFuncGetAttributes
directed_tests/runtimeApi/module/hipExtLaunchMultiKernelMultiDevice
directed_tests/gcc/LaunchKernel

Change-Id: I52135b61e8283eb4f9f10f77895151e4e55418d9


[ROCm/hip commit: d967be8eeb]
2020-03-26 23:28:35 -04:00
Sarbojit2019 9e98e69b7a Fix for segfault seen if invalid kind is passed to hipMemcpy (#1937)
Fixes SWDEV-224941

[ROCm/hip commit: 3e363047d5]
2020-03-26 17:04:43 +05:30
Jatin Chaudhary 26b7d3e2ee [dtest] Adding VectorTest (#1732)
Adding unit test for operations of device vector types

[ROCm/hip commit: ee5fa8977c]
2020-03-26 17:03:43 +05:30
jujiang 910a8a5d1e SWDEV-226708-hipMemcpyPeerAsync failed-->Update test app to create stream on proper device
Change-Id: Ia9f51435ffb5a8fbbff39e363acecabb338bf34c


[ROCm/hip commit: 3774a1b106]
2020-03-25 17:22:56 -04:00
Vladislav Sytchenko a48ad08f24 Disable failing tests for VDI
The hipExtModuleLaunchKernel and hipModuleLoadDataMultiThreaded tests keeps randomly failing on Jenkins.

Change-Id: I87e5d54fb7429c14ff1dcecb20e03a7816670fae


[ROCm/hip commit: e7d91b8230]
2020-03-23 17:09:57 -04:00
Jeff Daily a2915ae475 fix hipStreamAddCallback, block future work on stream (#1934)
[ROCm/hip commit: 01d661b159]
2020-03-19 16:16:04 +05:30
Sarbojit Sarkar 771fb00972 Enable VDI Occupancy test
Change-Id: Ia89155ca909b9b7346584d19962fa0a94033bb17


[ROCm/hip commit: 3baff10618]
2020-03-19 10:43:40 +05:30
Sarbojit Sarkar ac7f37d9c3 Merge "[hip-vdi]Fix for TF build failure [SWDEV-225827]" into amd-master-next
[ROCm/hip commit: 0a35286988]
2020-03-18 11:52:46 -04:00
Jatin Chaudhary a9bccfb6b2 Merge "Enable saxpy Test" into amd-master-next
[ROCm/hip commit: b68b2884ba]
2020-03-18 06:32:05 -04:00
Sarbojit Sarkar 4135ec890a [hip-vdi]Fix for TF build failure [SWDEV-225827]
Change-Id: I8478779bef92bad8353b8d066b28c220bb59b98d


[ROCm/hip commit: 82926666c4]
2020-03-17 22:52:01 -04:00
Vladislav Sytchenko ac1cc9bacd Enable simpleTexture2DLayered test for VDI
Change-Id: I420f68824c6825152ac50e5a129b11b6ad88deb9


[ROCm/hip commit: 1b288456ae]
2020-03-17 17:50:46 -04:00