AI/rocm-systems
2
0
Bifurcation 0
Code Tickets Demandes d'ajout Actions Paquets Projets Publications Wiki Activité
6 822 Révisions 3 Branches 0 Étiquette
ea5838320e31a7810bdca18be19da29da296a049
Graphe des révisions

6822 Révisions

Cette branche
Cette branche
Toutes les branches
Auteur SHA1 Message Date
sdashmiz ea5838320e SWDEV-379388 - remove check for all streams done 
- cuda shows  a different behaviour and different error need more
  investigation

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: I68771102ba4dff6157bca34a4135cb245f023d08
 2023-02-23 22:56:23 -05:00
German Andryeyev 314bdba632 SWDEV-353281 - Add support for MemPool in graphs 
Implement hipDeviceGetGraphMemAttribute, hipDeviceSetGraphMemAttribute
and hipDeviceGraphMemTrim

Change-Id: I4f8fc1250ce1e8b7636d43d59ba7343158e45088
 2023-02-23 12:49:53 -05:00
Sarbojit Sarkar d0920c5959 SWDEV-293749 - Fix for operator mixup 
Change-Id: I61d1fea5a6ed2176dd92050c6d96cee1af3a39fb
 2023-02-23 04:45:23 -05:00
Anusha GodavarthySurya 32a9249d3e SWDEV-345571 - Added support for half/half2 data types for warp shuffle functions 
Change-Id: I276a55129d6527b73292d75eb18403acd2623c8a
 2023-02-22 22:40:01 -05:00
Saleel Kudchadker 7fc5ae2226 SWDEV-364604 - Add support for hipEventDisableSystemFence 
Change-Id: I1a6451c873fb22729ac61e4e80f8531251e990f0
 2023-02-21 23:11:40 -05:00
pghafari c221406681 SWDEV-366520 - DLL_PROCESS_DETACH update 
making sure the current thread is not null before calling ihipDestroyDevice

Change-Id: Ib75e3f9ee1c4e0065986e3fed1065907220f4379
 2023-02-21 23:02:24 -05:00
Jaydeep Patel 0ad47eb3e5 SWDEV-319526 - SE ID size incresed. 
Change-Id: Ia7df94d172102b321f12c8caa821e3a7e4447a21
 2023-02-21 22:13:57 -05:00
Ioannis Assiouras e3633dc8f4 SWDEV-381402 - Derive hip::Stream from amd::HostQueue 
Change-Id: I6c1aca5eb350c32d974ae4ffcc725705355956d8
 2023-02-21 18:12:03 -05:00
Ioannis Assiouras aaf1c19609 SWDEV-384362 - Added explicit cast from __fp16 to _Float16 in rcph 
Change-Id: Ibbb11e928a80126ed7a8c7cd8bddebc74c38986d
 2023-02-21 17:32:59 -05:00
Yaxun (Sam) Liu cbb3937196 SWDEV-380145 - [GFX][CQE] Mathlibs and Blender build failed in both RT and CPL Jobs 
Remove --hip-device-lib-path from hip-config.cmake
and let clang determine device lib path

Change-Id: Ice009875624692bc2895020c9577b94ddbd6840f
 2023-02-21 15:33:22 -05:00
Ajay fc6a77a09f SWDEV-384100 - HIP support for CUDA 12.0 
Apps are failing to build due to undefined deprecated texture APIs

Change-Id: I1fb64adc4bc0ba6ee6ecaa65d54b34da0327e6a3
 2023-02-21 12:23:48 -05:00
Rakesh Roy 348698ed30 SWDEV-377782 - Fix segmentation fault for hipLaunchKernel 
- If fat binary doesn't contain code object for current gfx then inside FatBinaryInfo::ExtractFatBinary(), valid FatBinaryDeviceInfo address isn't stored in vector fatbin_dev_info_
- This raises segmentation fault during hipLaunchKernel

Change-Id: I21017338d91edbd5d9cc2d37277f66558198a129
 2023-02-20 09:54:44 -05:00
Konstantin Zhuravlyov caf7551dd7 SWDEV-1 - Add missing gpu cases in getProcName 
Change-Id: I16103ab213cc70f388690df85e6a03e7a408384d
 2023-02-17 15:55:09 -05:00
victzhan d6a08403d8 SWDEV-376995 - Fixed misplaced checking 
Change-Id: Ia3bddabfa7fc76066541fb81723136ae6cffb0a4
 2023-02-17 13:34:51 -05:00
Rakesh Roy 287d07ccd4 SWDEV-338733 - Implement hipArrayGet* APIs 
- Add implementation for hipArrayGetInfo, hipArrayGetDescriptor &
  hipArray3DGetDescriptor APIs

Change-Id: I181a472066006bc3bd0d987408ea67e218310983
 2023-02-16 23:04:29 -05:00
Ioannis Assiouras 8b87ccb8cc SWDEV-381402 - convert host_device to host_context of type amd::Context* 
Change-Id: Ic1cb9a3fa64e16699fad7e9ec6679f1d34b14bef
 2023-02-16 17:49:12 -05:00
kjayapra-amd 193c5e387e SWDEV-376697 - Pass uncached memory flag when hipDeviceMallocUncached memory is requested. 
Change-Id: Idc12948047fdb69876e31edf34a8bcda46c9c303
 2023-02-16 14:05:54 -05:00
kjayapra-amd 68139f9ddb SWDEV-381898 - Move the lock after code object loading since COMGR is thread safe now and VDI also have locks. 
Change-Id: I15547f3ae3711d12a1ddf5cb7e9abd40a95ded89
 2023-02-15 10:23:28 -05:00
Maneesh Gupta 2801be2372 SWDEV-366831 - Revert "File reorg backward compatibility message changed to #error" 
This reverts commit 810c4ac244.

Reason for revert: Need app fixes first

Change-Id: I1fea9a2ca8d57ef79a4f407bbc0d906976292eb1
 2023-02-14 22:55:40 -05:00
victzhan 4e324a9c63 SWDEV-376995 - Added if statement so that when AQL dispatch failed it returns corresponding hip error instead of hipSuccess 
Change-Id: I0724fbcf0833c5dd8b2e4d6e443b3e226046dddf
 2023-02-14 14:30:50 -05:00
sdashmiz e34be4fbee SWDEV-377862 - wrong format for memcpy1d 
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Ide6d252083b1812b0ad9cd182b1435e3e59b3aa1
 2023-02-14 09:47:04 -05:00
Sourabh Betigeri 191b468d89 SWDEV-375194 - Fixes graph dot file descriptions to include labelId matching CUDA 
Change-Id: Ia0e6b77e38678b13457f86755ed8f3b852c9b7a1
 2023-02-13 19:43:12 -05:00
Sourabh Betigeri 4cbf9a4a16 SWDEV-375202 - Fixes print formatting for flags in hipGraphDebugPrint() to match CUDA 
Change-Id: I2d85fc38d2c65bc12534109883fe00802e77e62d
 2023-02-09 13:07:57 -05:00
Ranjith Ramakrishnan 810c4ac244 SWDEV-366831 - File reorg backward compatibility message changed to #error 
Change-Id: I44adb1a4b9bba0bd89edb75be715504ede2e3d08
 2023-02-09 12:46:13 -05:00
Satyanvesh Dittakavi 99556449b6 SWDEV-370552 - Correct the HIPRTC behavior to optimize the ISA only once 
Change-Id: Idaf0ea8294657db3666e9548deb6a9629e0ee718
 2023-02-09 11:55:41 -05:00
sdashmiz 5c5b220561 SWDEV-374378 - correct setparam for memcpy node 
- params should be valid when used for default flag since we support
  unified virtual address space

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: I75d40e437b12ee58e72e423bb4818b484ce35b66
 2023-02-09 09:39:20 -05:00
Saleel Kudchadker 2e4ce59cf4 SWDEV-381633 - Better log 
Change-Id: I5c59d42462fe8a233ef10e26ec67314219aeb167
 2023-02-08 10:21:57 -08:00
Jaydeep Patel e940beb459 SWDEV-380405 - Check for invalid stream for hipMemcpyPeerAsync. 
Change-Id: I6dfccb4d20bb638bd596c071030c68889743d706
 2023-02-08 00:47:35 -05:00
pghafari 03f62b90ef SWDEV-377571 - adding scopelock for hipDeviceReset 
Change-Id: I3dd95a40d6abff721a4774f26e99d1162bafdfa1
 2023-02-07 11:29:20 -05:00
Matt Arsenault eacf63673b SWDEV-1 - Use proper __builtin_amdgcn_rcph builtin 
Change-Id: Ic0b1b25a5ab7d132cb51425f2a17bc779c762668
 2023-02-07 10:58:48 -05:00
Matt Arsenault bebbf3c4ec SWDEV-1 - Eliminate rcp_2f16 pseudo intrinsic 
No such wrapper or intrinsic would ever exist because there is no such
underlying instruction.

Change-Id: I6c3f64cd2df2a58edf32037da8f5712868f296ea
 2023-02-07 10:58:31 -05:00
Ioannis Assiouras 6704f3d0f0 SWDEV-380687 - Fixed typo in safe atomicAdd for gfx90a 
Change-Id: I87bc6d9e0ef1f564d679c6280c71c4633d3aa619
 2023-02-07 10:14:34 -05:00
Ioannis Assiouras 24d3d8216b SWDEV-380466 - Fixed typo in unsafe atomicAdd for doubles and gfx940 
Change-Id: I3b9ea4773f94bf6a9b9dfb655062f42aeb3b5eba
 2023-02-07 10:06:17 -05:00
Jaydeep Patel 5f231c55e3 SWDEV-380405 - Make hipMemcpyPeer async w.r.t. host and let dst device wait till copy finishes by src device. 
Change-Id: Idbe25404d0c31b93436e190b548f12f327f47a04
 2023-02-07 00:34:45 -05:00
German Andryeyev 0fe03b6494 SWDEV-353281 - Switch Graph to operate with stream 
MemPool was designed to use hip::Stream, but graph implementation uses
amd::HostQueue. Hence switch graph to hip::Stream management.

Change-Id: Ia319389de45e4c3c6043d17473279a6f27a13140
 2023-02-06 10:11:55 -05:00
Matthew Arsenault 8c7391398a SWDEV-1 - Reapply "SWDEV-1 - Directly call __builtin_amdgcn_fence" 
This reverts commit 5b39c346ad.

Resubmit after https://github.com/ROCmSoftwarePlatform/rocPRIM/commit/ba8a86166ec9c4cf3a40ecde7017feeb1484e7f6

Change-Id: I194559484a5a0d7f4443381fe77218ea73d2def9
 2023-02-03 10:54:27 -05:00
Jaydeep Patel 01c3299425 SWDEV-379395 - Use getQueue as it handles null stream and flags can be combination. 
Change-Id: If37854a9fc0fc57acb30e652953a7f283831cad8
 2023-02-01 12:03:42 -05:00
Jaydeep Patel f9e27bcdd4 SWDEV-377804 - Initial commit to support hipGraphInstantiateFlagAutoFreeOnLaunch 
Change-Id: I7a35becb6c98a6ff70264e141317d98be7457a37
 2023-02-01 11:51:39 -05:00
Matt Arsenault 14477c24d0 SWDEV-1 - Use proper builtins for math intrinsics 
Change-Id: If0e420332c718abe0e9f6316c467b6b29b80b183
 2023-02-01 07:19:45 -05:00
sdashmiz 34d087da93 SWDEV-361623 - correct remove edge behaviour 
- remove node dependency before checking parents
- reduce edge level acording to new value of node

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Id4bff1684f7e0b42beeebc4d2e009bfdb507fb5f
 2023-01-31 12:48:59 -05:00
Rahul Garg 118e7144f8 SWDEV-379678 - Remove catch build option 
Change-Id: Idedf5e61da1e6c7fbdd9a65e57220875a3b24112
 2023-01-30 11:04:03 -05:00
sdashmiz b251c8fdb2 SWDEV-374368 - dependency list should not have duplicate 
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: I67e1c8203f10916b98408e2004e6c64e96b1933b
 2023-01-30 10:28:35 -05:00
sdashmiz 23edcd3e23 SWDEV-374389 - correct update dependency behaviour 
- nodes should belong to graph
- num of passed dependency cant be larger than graph nodes

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Ia6f2283546bc44edee705b0483bfe506b7b1177a
 2023-01-30 10:05:52 -05:00
Ajay GunaShekar 1f4176062b SWDEV-372757 - Don't destroy null queue in MT 
This reverts commit f39655c0c8.

Reason for revert: patch does not fix all stream hangs. So another patch was merged which fixes all issues.

Change-Id: I332d1ea29c23747b46b7667fe3e34e0ceefd2b23
 2023-01-25 23:41:16 -05:00
sdashmiz a4dd362a1d SWDEV-379151 - correct error status 
- if the stream is null ptr and there is capture ongoing return an error

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Iff33e4aebc253fb7bb56daf5c455722d726c6705
 2023-01-25 15:06:38 -05:00
Rakesh Roy 8b00f56577 SWDEV-375004 - Fix rocprim test failure 
- For !__HIPCC_RTC__ case, operator<<(std::ostream& os, const hip_bfloat16& bf16) calls itself in endless recursion
- Convert hip_bfloat16 to float to fix this

Change-Id: I252a656817550caf43c587cebf461474f12b8c0c
 2023-01-25 00:01:02 -05:00
Jaydeep Patel 70bfc6145b SWDEV-379125 - Check only if there is attr set for graph kernel node. 
Change-Id: I8768b33ad27e75eb753d99d682edf60b31b240df
 2023-01-24 09:51:12 +00:00
Satyanvesh Dittakavi 0ccd41050b SWDEV-372396 - Address the errors in hiprtc headers with -Werror 
Change-Id: Ied553216dfc2ff8b5c72de617cb47b6ca8f52063
 2023-01-23 17:25:42 +00:00
Maneesh Gupta 5b39c346ad SWDEV-378321 - Revert "SWDEV-1 - Directly call __builtin_amdgcn_fence" 
This reverts commit 3e54bad5b3.

Reason for revert: Root cause for regression SWDEV-378321

Change-Id: If3116c5ad1a23db1840e5fc019d2fe997b37d229
 2023-01-19 13:01:27 -05:00
German b685930bee SWDEV-377991 - Rmove Liquidflash logic 
Change-Id: I1c2169c1a8c7449c59cc15074af039c48fc1ef31
 2023-01-19 09:58:07 -05:00