AI/rocm-systems
2
0
Vork 0
Code Kwesties Pull-aanvragen Actions Paketten Projecten Publicaties Wiki Activiteit
12.543 Commits 3 Branches 0 Labels
6926183974f2c72c3cf5e49829a44d42e72b1439
Commit grafiek

6367 Commits

Auteur SHA1 Bericht Datum
Ajay 6926183974 SWDEV-418100 - HIPNV_DIR error for nvidia build 
Change-Id: Id1fb67311fb6a0af98de7c2dcef5cfcf29102d14
 2023-10-23 18:04:05 -04:00
Saleel Kudchadker 5662d4037c SWDEV-408180 - Address possible cornercases 
- Address corner cases that can arise with the new
hipMemcpyDeviceToDeviceNoCU enum
- Better log

Change-Id: I6035b901f8d616741054b7a5ff4f67956329ac57
 2023-10-23 16:54:08 -04:00
kjayapra-amd e226ae109b SWDEV-413997 - Fixing multiple access desc cases for hipMemSetAccess. 
Change-Id: Iec7d1207ec0a7136e4e74ef2e390f3347e753d40
 2023-10-23 09:44:04 -04:00
Jaydeep Patel ee00ebc42f SWDEV-425568 - Do cpu wait for device sync. 
Change-Id: Ia05e09bd10ab623b36c74037e9988e132120dd9f
 2023-10-21 01:16:06 -04:00
Saleel Kudchadker f316a30e5d SWDEV-408180 - Add a new hipMemcpyKind 
Add hipMemcpyDeviceToDeviceNoCU to force a non blit copy path. This
helps in cases where an app may determine that CU may be busy and copies
with SDMA may be quicker.

Change-Id: I59b415dd8f6022c244e8d75f265464d5c635df1e
 2023-10-20 13:18:10 -04:00
taosang2 5a0085e516 SWDEV-364236 - Fix layered Image issue 
Fix wrong logic to get layer index;
Make layered image's layout match cuda spec;
Fix wrong comparision of element size.
Remove amd::BufferRect from ihipMemcpyAtoHCommand()
and ihipMemcpyHtoACommand().
Change-Id: Icc6a4233fbce2e9b2dc6feb79e6bfbd761684c7d
 2023-10-19 16:06:20 -04:00
German 694fe4bedb SWDEV-427689 - Report LUID in Windows 
Pass LUID infromation from PAL to HIP device properties.
NodeMask is calculated based on the order of devices in PAL

Change-Id: Ic53707b68b16f392e5284a0105bf1f3941b46653
 2023-10-18 15:07:39 -04:00
taosang2 0ca61130a2 SWDEV-426270 - Remove duplicated operators 
Remove duplicated operators of hipComplexFloat and
hipComplexDouble.
If users need complex number multiplication and division,
they should call
hipCmulf() and hipCdivf() for hipComplexFloat,
hipCmul() and hipCdiv() for hipComplexComplex

Change-Id: Ie58d1642d578e7118997db40a9fd6a6641b666fd
 2023-10-18 14:56:32 -04:00
Jatin Chaudhary 56f3b2563c SWDEV-306642 - Move the deprecated function/struct to hip_device_deprecated.cpp 
Change-Id: Id1f8db09271c537a200bc090ba1feaacfb023b88
 2023-10-16 21:42:18 +01:00
Satyanvesh Dittakavi 353dbe6e3b SWDEV-419480 - HIPRTC implementation of standard headers shouldn't be in std namespace 
HIPRTC implementation of few type traits are defined in std
namespace which causes conflicts with the std C++ headers when
apps try to include those std headers. Instead, use the
specific implementation of these headers from __hip_internal
namespace to avoid this.

Change-Id: Ia358df159af8783d1eba9a19cd458e192bf7e9e6
 2023-10-16 13:10:55 -04:00
kjayapra-amd 3ef829939a SWDEV-413997 - Initial VMM changes for ROCm path. 
Change-Id: I4405fd7b53182eb4c4622835c811c0dc08461537
 2023-10-16 11:29:16 -04:00
Rahul Garg 8fe1d9dda1 SWDEV-415029 - [ABI Break] Remove hcc symbols 
This reverts commit 2535fac296.

Reason for revert: Bring back original change

Change-Id: Ie20e80f6e9b7d67a28e3a255abaf82018eb61e7a
 2023-10-16 07:34:43 -04:00
sdashmiz 2d83abaca6 SWDEV-389530 - [ABI Break]Match error with cuda 
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Id9de54b4fd1be7b6b887a4ebfcc6a3d9a70c7bc9
 2023-10-16 07:31:34 -04:00
sdashmiz d78aef7f66 SWDEV-371332 - [ABI Break] Return success for unregistered ptr 
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Ie58d16420578e7118997eb40a9fd6a6641b666f3
 2023-10-15 14:32:24 -04:00
Maneesh Gupta 67dda1ffd6 SWDEV-418100 - Move nv headers to hipother repo 
Change-Id: Ib54546e366b61bdb83789d8264f30f1bfb875605
 2023-10-14 06:56:13 +00:00
Jaydeep Patel 7150b2eaad SWDEV-425490 - Move ptrdiff_t & clock_t to hiprtc.cmake. 
Change-Id: I7c8ce3c1b8cb11e0253b0f51ae10fca7f0a32017
 2023-10-13 00:58:56 -04:00
sdashmiz c089ef4a2b SWDEV-332969 - [ABI Break]Substitute hipArray* with hipArray_t 
- hipArray will be an internal struct from rocm6.0

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Icf97fe96b87be8532098cd7f9ceaad099f99c9b9
 2023-10-12 12:09:19 -04:00
Jatin Chaudhary 2989840511 SWDEV-306642 - [ABI Break] Add texture/surface/device capabilities device struct entries 
- alias hipGetDeviceProperties to hipGetDevicePropertiesR0600
- alias hipDeviceProp_t to hipDeviceProp_tR0600
- remove gcnArch from new device property struct
- add new requested struct members

Change-Id: If3f5dbef3d608487d9f6f419285f4bf577ea9bf0
 2023-10-12 11:16:18 -04:00
jiabaxie 813907c29d SWDEV-418999 - python script to support profiler with hip versioning 
Change-Id: I8f5ad81162581bf3792c2606ba8c6c3a8e0b4bf2
 2023-10-11 13:46:45 -04:00
Rakesh Roy 52001adf43 SWDEV-421667 - Print shared library name which doesn't contain CO for current device 
- ML Frameworks link many ROCm component libraries
- It becomes a tedious task to figure out which library HIP is complaining about
- To improve debuggability print out the shared library name

Change-Id: I53c4d66393670356b8cafd3e48075e430f0a45ce
 2023-10-11 10:43:03 -04:00
Anusha GodavarthySurya c7e4e9c2f4 SWDEV-408701 - Avoid adding duplicates when no node is captured in cross stream 
Change-Id: Iccbddaf9db73238aa938f8b3e8ec410f4a86d524
 2023-10-09 13:15:47 -04:00
Rakesh Roy 2535fac296 SWDEV-425967, SWDEV-425968 - Revert "SWDEV-415029 - [ABI Break] Remove hcc symbols" 
This reverts commit 051e1005f4.

Reason for revert: This causes build failure in hipBLASLt & hipSPARSELt

Change-Id: I59f6aeb8b82261b77eb978e53407bc56be1d0cf1
 2023-10-09 06:30:19 -04:00
Sourabh Betigeri 01aa3557f4 SWDEV-369792 - Fix to use the roclr context already created when creating hip::Device rather than creating a new context in hip 
Change-Id: I6dbccb1a17dee0e9a72ec52cb1a5bb096315fa0f
 2023-10-07 14:32:32 -04:00
Jaydeep Patel 46de4256e0 SWDEV-425490 - ptrdiff_t differs on windows and linux. 
Change-Id: I5b943e869a6552870aa268be898182e806161b3c
 2023-10-06 16:04:52 -04:00
Ioannis Assiouras 43126bc19b SWDEV-420989 - Initialize tiled_info meta_group_rank and meta_group_size 
Change-Id: I6792e928702d0fef81f18e74eaead3ad3a8fbb7b
 2023-10-06 05:43:04 -04:00
Satyanvesh Dittakavi f64ead62be SWDEV-424273 - Address MIGraphX tests staging failure 
Change-Id: I5f51b62a0046f567603008974fda029d40d7656b
 2023-10-05 15:55:54 -04:00
taosang2 6398f604b0 SWDEV-299127 - Support External Mipmap 
Support hipExternalMemoryGetMappedMipmappedArray().
Add ImageExternalBuffer to differiate ImageBuffer.
Currently we only support tiling_optimal mode as
vulkan driver doesn't provide tiling information.

Change-Id: I7e3524cdde53e4df9f728894bcebf4bd3f58d4d9
 2023-10-05 09:58:17 -04:00
Anusha GodavarthySurya e63c280d4d SWDEV-422207 - Capture AQL Packets for graph Kernel nodes during graph Inst. And enqueue AQL packet during launch 
Change-Id: I1e5f7f9e2a70bd500d190193cb6ba0867f5a63e7
 2023-10-05 00:34:29 -04:00
Julia Jiang 3eb46ae588 SWDEV-425362 - Fix GL section on HIP API module 
Change-Id: I6824758a4744739a596a96e04053eec8e16516cc
 2023-10-04 14:26:45 -04:00
Jatin Chaudhary ab6d34ae77 SWDEV-420894 - Remove directed test link from CMakeLists.txt 
Change-Id: Iece57a1624b921d556a300c8f442ee12fd8a4948
 2023-10-04 05:01:49 -04:00
Ioannis Assiouras bf31109241 SWDEV-425129 - Revert "SWDEV-420822 - [ABI Break] Merge hipFunction_attribute into hipFuncAttribute" 
This reverts commit c469f18e91.

Change-Id: I02d6e77f0874fc37f22de267435917edd4fdede3
 2023-10-03 11:32:19 +01:00
Ioannis Assiouras c469f18e91 SWDEV-420822 - [ABI Break] Merge hipFunction_attribute into hipFuncAttribute 
Change-Id: I9b9f7979e9b8dd422d9064c17c79a25bf7248d30
 2023-10-01 06:52:12 -04:00
Ioannis Assiouras ae9a956fd3 SWDEV-398472 - [ABI Break] Added new include file for openGL interop APIs 
Change-Id: Ic6debaadbffd6e773015cb365943bd0ae6f71966
 2023-09-30 11:46:32 -04:00
Ioannis Assiouras 31201b6e25 Revert "SWDEV-414194 - Make hip-lang available on nvidia platform" 
This reverts commit 97403db468.

After changes in upstream cmake hip-lang-config.cmake will not be required on nvidia platform.

Change-Id: I711601dac1064ea17f58437da8ffbc50678eda08
 2023-09-29 06:07:53 -04:00
kjayapra-amd c3a39ef32a SWDEV-424569 - Fixing a merge error, which removed amd::Program->release(). 
Change-Id: Ib43dfc528ce217cb23d5eb38a0f87c241ae274a6
 2023-09-28 11:41:04 -04:00
Ajay 3337f6912d SWDEV-1 - fix build errors for file descriptor 
Change-Id: I38b3962744f20ce758c32077f2c725013c666a35
 2023-09-27 20:00:05 -04:00
Satyanvesh Dittakavi f5a9a36cf3 SWDEV-421415 - Pass the right hip major, minor versions to hiprtc builtins 
Change-Id: I2ff5787039891d1d3390c996d37bf342e0a88705
 2023-09-26 00:52:54 -04:00
Jatin Chaudhary 0668f20780 SWDEV-410898 - Add includes in files that use them 
Change-Id: I14d9ea233d57c7267da3f9688305b949ced71a53
 2023-09-25 08:45:22 -04:00
Satyanvesh Dittakavi 2764b85ca5 SWDEV-402080 - Add options such as -Rpass=inline to exe_options in RTC if the user passes it 
Change-Id: I12fcf200ed9d3112b014f3d426d5fe504eeca163
 2023-09-25 04:03:44 -04:00
pghafari 9008a53c98 SWDEV-414833 - adding hipDeviceAttributeIsLargeBar 
to hipDeviceGetAttribute

Change-Id: Icde0ab9326b1759c66f9a3acbadfb9a01cf6a5be
 2023-09-25 00:31:30 -04:00
German Andryeyev fbea58ba11 SWDEV-423317 - Enable GPU wait for hip sync calls 
hipStreamSynchronize and hipDeviceSynchronize won't longer wait
for CPU commands in DD mode

Change-Id: I079c8bbfc34ddc6d3e2d74c92a34665877e512a5
 2023-09-22 13:04:27 -04:00
Jatin Chaudhary 49bb6a4072 SWDEV-421819 - Add ptrdiff_t and clock_t. 
Rework types inside new __HIP_NO_STD_DEFS__ guard

Change-Id: I2b67381c01ba497b323864afe0a8d1402e396748
 2023-09-22 05:07:52 -04:00
pghafari 96f41fad07 SWDEV-369567 - [ABI Break] updating gridY and Z max dimension check 
Change-Id: If515fda4938d3c5f455a02b4a65adaad76dc0aed
 2023-09-22 04:52:27 -04:00
sdashmiz 8705322f10 SWDEV-330665 - [ABI Break] check for attribute 
- Add support for DevAttrHostRegisterSupported

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Ica8d323eda97b65ef0088aa99c84dd36cfe4edf3
 2023-09-22 04:51:24 -04:00
Satyanvesh Dittakavi 16fb3ca923 SWDEV-407358 - Address MIGraphx -Werror issue with unsafe buffer access 
Change-Id: If4189dfbf12b670af60782f09ff8cf9b9867c299
 2023-09-22 04:50:32 -04:00
Ioannis Assiouras fe2d747bcc SWDEV-401489 - [ABI Break] Removed hipModuleLaunchKernelExt 
Change-Id: I0b31d9db755f8a89ead203dbd238a93c18b76855
 2023-09-21 23:50:16 -04:00
kjayapra-amd 369fdc4d87 SWDEV-422580 - Adding pcie.function to the PCI address string in hipGetDevicePCIBusId. 
Change-Id: Iaa73b6028ac7b1d05cc310405d6fe622d764320f
 2023-09-21 12:22:05 -04:00
Sourabh Betigeri 3f88fe850b SWDEV-326798 - [ABI Break] Fixes null stream sync behavior 
Change-Id: I84ad21f61779145c198dc68bf0fe02a57d34bf64
 2023-09-21 11:57:58 -04:00
Jatin Chaudhary 15ba5c0004 SWDEV-422808 - Add E5M2 and E4M3 for nvidia headers 
Change-Id: Ib40e75c1b2e18d75164607a46e95fc322363c08e
 2023-09-21 11:57:04 -04:00
Satyanvesh Dittakavi f16d336e32 SWDEV-375607 - Fix hipGraphExecUpdate behavior 
Addresses the below scenarios like parameters mismatch
in memcopy node, difference in the count of nodes, difference
in the dependencies of the nodes.

Change-Id: I31c6516fb27cc1007809f1b50306fdb0c2356ccc
 2023-09-21 11:17:49 -04:00