Grafico dei commit

1046 Commit

Autore SHA1 Messaggio Data
kjayapra-amd fb0c0122af SWDEV-236178 - Remove __hip_pinned_shadow reference from dtests and add hipModuleUnload for all corresponding hipModuleLoad calls.
Change-Id: I405789b430ffbb8fccda1cebdb5d18e83a85c926


[ROCm/clr commit: 3fab381493]
2020-06-11 22:34:36 -04:00
kjayapra-amd d6ccf1209c SWDEV-236178 - Reorganizing Platform/Modules code for easy access.
Change-Id: Ie8920260ffc4ff01e44b48af8cec9ea5aed1aa9b


[ROCm/clr commit: 840347f0d0]
2020-06-11 10:11:20 -04:00
Christophe Paquot 4206cfddc5 Do not deferred stream creation now that we multiplex HW queues
SWDEV-239856

Change-Id: I156650faf832f86891f00ee167269509edd844ec


[ROCm/clr commit: 20ae4d709f]
2020-06-09 19:16:25 -04:00
Jason Tang 7735b228ec SWDEV-227909 - Add gcnArchName
Change-Id: Iea6d16b5d693dd0d900fa424d7a321c39315430e


[ROCm/clr commit: 14c699e9de]
2020-06-05 15:33:55 -04:00
rohit pathania 16af0aebc0 [ dtest ] hipModuleLaunchKernel multiThreaded n multiGPU scenarios
1.Added hipModuleLaunchKernel multithreaded multi GPU scenario.
2.removed hipCtxCreate API from earlier test as it is deprecated.

SWDEV-238517 for enhancing hip unit tests

Change-Id: Id102d80887b6ff61a59938dbeb9fa2a26a3275b2


[ROCm/clr commit: 0920bac577]
2020-06-05 09:40:58 -04:00
Lakhan Singh Thakur bedadf571d [dtest] merge 'Adding the two test cases to cover scenarios observed in SWDEV-181598.'
SWDEV-238517 for enhancing hip unit tests

Change-Id: Ie61145b46c89b2e970af0ab11e22b6f6286ec90f


[ROCm/clr commit: 6f87616103]
2020-06-05 09:10:23 -04:00
Payam 8bdf07bb9c Observed softhang while running hipStreamAddCallbackCatch SWDEV-236746
Workaround hipStream deadlock issue as the same lock was used twice SWDEV-236746

Change-Id: Icc60104ce6edf4cfd2a3a889bab78a6caadd50b7


[ROCm/clr commit: f3ee29cdb2]
2020-06-04 14:11:22 -04:00
Siu Chi Chan 1f7c745330 add constexpr constructor for vector types
Change-Id: I45bb0537d6a24ee50b548c2fd8b4f20518764813


[ROCm/clr commit: 4b56aaefd6]
2020-06-04 01:57:03 -04:00
Aaron En Ye Shi b2f9e1c299 Add compiler-rt library for __fp16 and _Float16
Similar to HCC, link with compiler-rt to support __fp16 and _Float16 type conversions in ONNX models. This should resolve SWDEV-238491.

Change-Id: Iad8dcff568831719f501f562a04023326ae8036c


[ROCm/clr commit: d93134e727]
2020-06-03 18:53:14 +00:00
Jatin 216873e9c8 Adding changes for hipExtLaunchKernel for rocCLR
Change-Id: Iba52bc3bde7c37f3fb375a55ba0947e87b3cdc9b


[ROCm/clr commit: 126573df4c]
2020-06-02 14:16:41 -04:00
Aryan Salmanpour 5aec64346f [dtest] add a multi stream test for (SWDEV-237846)
Change-Id: I4a1d764df75af7019d0f38313e5e0a6a224818f8


[ROCm/clr commit: 200ab30084]
2020-05-28 23:36:10 -04:00
Aryan Salmanpour 71d0954669 [dtest] add a test for hipExtStreamCreateWithCUMask API
Change-Id: Ib567e559c5ab7d04ac5c300fd7e15eedfc4fb6e6


[ROCm/clr commit: c9b8a19ce0]
2020-05-26 18:15:09 -04:00
Mahesha Shivamallappa 871ac22d36 Add support for cooperative group type - thread_block
Change-Id: If3770b6d6718a638b70f527ae2533d9ef3267ff4


[ROCm/clr commit: f4e6dec3ac]
2020-05-22 23:08:42 -04:00
Vlad Sytchenko b0a332e466 Reenable texture reference tests
Change-Id: I77024476cff77951d61dc48f7e30094d6b47266c


[ROCm/clr commit: 355661b5da]
2020-05-22 14:13:50 -04:00
German Andryeyev 9f69856aa4 Add a test case for async double memset
Change-Id: I8a1df610c8d3d942651f258e7812e8697067c347


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


[ROCm/clr commit: e1961c838f]
2020-05-16 02:38:14 -04:00
German Andryeyev 1f5fc3cb04 Merge "Correct mgpu coop launch test" into amd-master-next
[ROCm/clr commit: a48ba48773]
2020-05-13 16:20:24 -04:00
German Andryeyev 2632fe42e5 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/clr commit: 999295b3fa]
2020-05-13 14:39:11 -04:00
Matt Arsenault 477012bf64 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/clr commit: 03ebfd2d49]
2020-05-11 15:20:58 -04:00
Tao Sang 4f8eff70ec 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/clr commit: f99c3ac337]
2020-05-06 14:06:07 -04:00
Payam 082b9e51ab name change vdi to rocclr
Change-Id: I06d198bbb4a499e153b290b73a92afed3553b252


[ROCm/clr commit: dba0e72de2]
2020-05-06 09:14:30 -04:00
agodavar 7da11623bd find_package(hip) changes for clang
Change-Id: I9dc1be1dd5f9424e26ebcd2961207e1c4467550f


[ROCm/clr commit: ce8a5af666]
2020-05-01 20:48:32 +00:00
root 6a7aa0c1c6 Merge master into amd-master-next
Change-Id: I3fc1dc0c860d627053537581e75561e8a7efe327


[ROCm/clr commit: b5031f39b1]
2020-04-26 22:19:37 +00:00
Yaxun (Sam) Liu c13a63bcff 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/clr commit: 29549ce4dc]
2020-04-24 12:30:28 -07:00
Yaxun Liu 80edc2b562 Merge "Enable template max and min for HIP-Clang" into amd-master-next
[ROCm/clr commit: 040ca11925]
2020-04-24 11:44:49 -04:00
Yaxun (Sam) Liu 066b79be84 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/clr commit: 1013e4eca8]
2020-04-24 09:51:17 -04:00
Tao Sang b0f72224a1 Add Performance/memory/hipPerfMemMallocCpyFree
Change-Id: Id1ac415f85028da3e9517c2226764bcb4acec1b1


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



[ROCm/clr commit: f2e1118d7a]
2020-04-23 09:12:06 -07:00
Tao Sang 98a2707931 Merge "support hipLaunchParm test with static lib of hip-vdi rt" into amd-master-next
[ROCm/clr commit: 8d63204887]
2020-04-21 15:54:46 -04:00
Tao Sang 672f243a42 Add perfDispatch tests into hip direct_tests
Port perfDispatch tests from OpenCL into hip direct_tests

Change-Id: I9f8362636e329d2d0a434c4f012ccc46a524c746


[ROCm/clr commit: b52873ff98]
2020-04-21 14:00:27 -04:00
Tao Sang 876c5c568e 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/clr commit: d27880ac39]
2020-04-21 13:55:42 -04:00
Michael LIAO f0df4418a0 [vdi] Refactor texture/surface reference support.
Change-Id: I8014d82aae7139ef5f95e4b50c4fc6da200dbc9d


[ROCm/clr commit: 441284841d]
2020-04-21 11:56:48 -04:00
Sarbojit2019 2436c2dd6f [HIPTEST]common changes for unittest (#2017)
[ROCm/clr commit: 7808be893f]
2020-04-17 10:31:47 +05:30
Jeff Daily 8b0a909b2b add IPC event support (#1996)
[ROCm/clr commit: e943144b31]
2020-04-17 10:31:22 +05:30
Yaxun (Sam) Liu 2406fa8a3d 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/clr commit: d556c3425b]
2020-04-14 16:07:14 +05:30
Yaxun (Sam) Liu aadb232c20 Fix MIOpen build failure
This is charrypick of 9ead991784
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/clr commit: 4e1d05c4be]
2020-04-13 23:01:31 -04:00
Maneesh Gupta 997cab12d3 Merge "Merge branch 'amd-master' into amd-master-next" into amd-master-next
[ROCm/clr commit: d02eb22c63]
2020-04-10 01:11:03 -04:00
Vladislav Sytchenko de96ecc441 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/clr commit: b291104e7d]
2020-04-09 14:02:40 -04:00
Maneesh Gupta e5ee180568 Merge branch 'amd-master' into amd-master-next
Change-Id: I3094c15008093f2072bcd38aca4ea90aeae2d97b


[ROCm/clr commit: 0ea6697192]
2020-04-09 06:31:00 -04:00
Sameer Sahasrabuddhe e2b46225c7 printf test: loop with divergent exit condition
Change-Id: I1071e4a240a280332bde669701c72228b9dea2df


[ROCm/clr commit: 7a51f9c5e8]
2020-04-09 10:20:11 +05:30
Evgeny Mankov 7fe43d9bc3 [HIP][HIPIFY] Remove HIPIFY related stuff due to moving of HIPIFY to a separate repo (#2002)
HIPIFY tools now are here: https://github.com/ROCm-Developer-Tools/HIPIFY

[ROCm/clr commit: 5d0ce39669]
2020-04-07 14:03:30 +05:30
Rahul Garg 63332172d6 Rename hipDrvOccupancy to hipModuleOccupancy and match CUDA syntax (#1943)
[ROCm/clr commit: 69e09a0b1b]
2020-04-07 14:02:52 +05:30
German Andryeyev bcb3769d7f Merge "SWDEV-184709 - support hipLaunchCooperativeKernel()" into amd-master-next
[ROCm/clr commit: 056a2d7227]
2020-04-06 11:45:34 -04:00
Sarbojit2019 77fd519260 hipEventElapsedTime should respect device (#1992)
Fixes SWDEV-228636.
Also added a unit test to verify this.

[ROCm/clr commit: 3523219b43]
2020-04-06 15:38:25 +05:30
ansurya 6b18a8e068 Initial support for bfloat16 (#1980)
[ROCm/clr commit: ff7aaedca2]
2020-04-06 15:35:43 +05:30
Sameer Sahasrabuddhe 3535475677 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/clr commit: 01d4117789]
2020-04-06 00:49:34 -04:00
German Andryeyev 8a6d893130 SWDEV-184709 - support hipLaunchCooperativeKernel()
- Enable cooperative tests for single and multiple devices

Change-Id: I54b6713f578b6b5e670f117b17469c0091028c99


[ROCm/clr commit: 2e948e4034]
2020-04-02 12:55:05 -04:00
ansurya 79c1ac76a4 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/clr commit: 68f1b814b1]
2020-04-01 12:10:17 +05:30
agodavar d329bd0684 Update Enable/Disable peers to match cuda behaviour
Change-Id: I67194ccf77a0019368579ff7d95b7790fcf228f3


[ROCm/clr commit: 96d119ac77]
2020-03-30 12:49:16 -04:00
Tao Sang 0e3a7ed058 Merge "Support hipFuncGetAttributes with hip-clang+Hcc RT" into amd-master-next
[ROCm/clr commit: b2afe3c250]
2020-03-27 14:36:41 -04:00