7239 Commits

Author SHA1 Message Date
Julia Jiang f77b4f705a SWDEV-425362 - Fix GL section on HIP API module
Change-Id: I6824758a4744739a596a96e04053eec8e16516cc


[ROCm/clr commit: 3eb46ae588]
2023-10-04 14:26:45 -04:00
Jatin Chaudhary e09e1594e8 SWDEV-420894 - Remove directed test link from CMakeLists.txt
Change-Id: Iece57a1624b921d556a300c8f442ee12fd8a4948


[ROCm/clr commit: ab6d34ae77]
2023-10-04 05:01:49 -04:00
Ioannis Assiouras dda3517ead SWDEV-425129 - Revert "SWDEV-420822 - [ABI Break] Merge hipFunction_attribute into hipFuncAttribute"
This reverts commit 1502016756.

Change-Id: I02d6e77f0874fc37f22de267435917edd4fdede3


[ROCm/clr commit: bf31109241]
2023-10-03 11:32:19 +01:00
Ioannis Assiouras 1502016756 SWDEV-420822 - [ABI Break] Merge hipFunction_attribute into hipFuncAttribute
Change-Id: I9b9f7979e9b8dd422d9064c17c79a25bf7248d30


[ROCm/clr commit: c469f18e91]
2023-10-01 06:52:12 -04:00
Ioannis Assiouras 3019f041c9 SWDEV-398472 - [ABI Break] Added new include file for openGL interop APIs
Change-Id: Ic6debaadbffd6e773015cb365943bd0ae6f71966


[ROCm/clr commit: ae9a956fd3]
2023-09-30 11:46:32 -04:00
Ioannis Assiouras 447ea938b9 Revert "SWDEV-414194 - Make hip-lang available on nvidia platform"
This reverts commit 14f3d8bcd6.

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

Change-Id: I711601dac1064ea17f58437da8ffbc50678eda08


[ROCm/clr commit: 31201b6e25]
2023-09-29 06:07:53 -04:00
kjayapra-amd 4937fa6b5d SWDEV-424569 - Fixing a merge error, which removed amd::Program->release().
Change-Id: Ib43dfc528ce217cb23d5eb38a0f87c241ae274a6


[ROCm/clr commit: c3a39ef32a]
2023-09-28 11:41:04 -04:00
Ajay a9e57c70b5 SWDEV-1 - fix build errors for file descriptor
Change-Id: I38b3962744f20ce758c32077f2c725013c666a35


[ROCm/clr commit: 3337f6912d]
2023-09-27 20:00:05 -04:00
Satyanvesh Dittakavi 43670ec526 SWDEV-421415 - Pass the right hip major, minor versions to hiprtc builtins
Change-Id: I2ff5787039891d1d3390c996d37bf342e0a88705


[ROCm/clr commit: f5a9a36cf3]
2023-09-26 00:52:54 -04:00
Jatin Chaudhary b624ca8896 SWDEV-410898 - Add includes in files that use them
Change-Id: I14d9ea233d57c7267da3f9688305b949ced71a53


[ROCm/clr commit: 0668f20780]
2023-09-25 08:45:22 -04:00
Satyanvesh Dittakavi 3c89a1a293 SWDEV-402080 - Add options such as -Rpass=inline to exe_options in RTC if the user passes it
Change-Id: I12fcf200ed9d3112b014f3d426d5fe504eeca163


[ROCm/clr commit: 2764b85ca5]
2023-09-25 04:03:44 -04:00
pghafari e9134ca616 SWDEV-414833 - adding hipDeviceAttributeIsLargeBar
to hipDeviceGetAttribute

Change-Id: Icde0ab9326b1759c66f9a3acbadfb9a01cf6a5be


[ROCm/clr commit: 9008a53c98]
2023-09-25 00:31:30 -04:00
German Andryeyev 2d492a201b 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


[ROCm/clr commit: fbea58ba11]
2023-09-22 13:04:27 -04:00
Jatin Chaudhary f62807d411 SWDEV-421819 - Add ptrdiff_t and clock_t.
Rework types inside new __HIP_NO_STD_DEFS__ guard

Change-Id: I2b67381c01ba497b323864afe0a8d1402e396748


[ROCm/clr commit: 49bb6a4072]
2023-09-22 05:07:52 -04:00
pghafari f088f06be6 SWDEV-369567 - [ABI Break] updating gridY and Z max dimension check
Change-Id: If515fda4938d3c5f455a02b4a65adaad76dc0aed


[ROCm/clr commit: 96f41fad07]
2023-09-22 04:52:27 -04:00
sdashmiz 0e64e42c60 SWDEV-330665 - [ABI Break] check for attribute
- Add support for DevAttrHostRegisterSupported

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Ica8d323eda97b65ef0088aa99c84dd36cfe4edf3


[ROCm/clr commit: 8705322f10]
2023-09-22 04:51:24 -04:00
Satyanvesh Dittakavi 9ee9f04cdd SWDEV-407358 - Address MIGraphx -Werror issue with unsafe buffer access
Change-Id: If4189dfbf12b670af60782f09ff8cf9b9867c299


[ROCm/clr commit: 16fb3ca923]
2023-09-22 04:50:32 -04:00
Ioannis Assiouras fb17aa5c41 SWDEV-401489 - [ABI Break] Removed hipModuleLaunchKernelExt
Change-Id: I0b31d9db755f8a89ead203dbd238a93c18b76855


[ROCm/clr commit: fe2d747bcc]
2023-09-21 23:50:16 -04:00
kjayapra-amd 142492d9eb SWDEV-422580 - Adding pcie.function to the PCI address string in hipGetDevicePCIBusId.
Change-Id: Iaa73b6028ac7b1d05cc310405d6fe622d764320f


[ROCm/clr commit: 369fdc4d87]
2023-09-21 12:22:05 -04:00
Sourabh Betigeri 5d160eb7ee SWDEV-326798 - [ABI Break] Fixes null stream sync behavior
Change-Id: I84ad21f61779145c198dc68bf0fe02a57d34bf64


[ROCm/clr commit: 3f88fe850b]
2023-09-21 11:57:58 -04:00
Jatin Chaudhary 6abb81112d SWDEV-422808 - Add E5M2 and E4M3 for nvidia headers
Change-Id: Ib40e75c1b2e18d75164607a46e95fc322363c08e


[ROCm/clr commit: 15ba5c0004]
2023-09-21 11:57:04 -04:00
Satyanvesh Dittakavi be8dbcf736 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


[ROCm/clr commit: f16d336e32]
2023-09-21 11:17:49 -04:00
Satyanvesh Dittakavi 78a3dc739d SWDEV-395996 - Add HIPRTC support for missing hip headers
hip headers such as hip_math_constants.h, library_types.h,
hip_common.h, channel_descriptor.h, device_functions.h, hip_complex.h,
hip_texture_types.h, math_functions.h, surface_types.h
are added in HIPRTC

Change-Id: I4a4c198449ceb609c3ff55e00b43056c1f085431


[ROCm/clr commit: d7d0f11318]
2023-09-21 03:11:06 -04:00
Ioannis Assiouras 7d69dd7598 SWDEV-416741 - Improve logging in find_package(hip)
Change-Id: Iaaaa595c668e5a8e977c9d2d31beca481748f637


[ROCm/clr commit: 5e51335ef6]
2023-09-18 19:10:38 -04:00
Ajay c9c3d951f2 SWDEV-421102 - make clr compatible with c++20
Change-Id: Ia692817232caa3ee97dc0b2139645a0474b582e1


[ROCm/clr commit: 2bae1b1387]
2023-09-18 11:28:29 -04:00
David Salinas f1325c1adf SWDEV-421615 - Correct required perl modules
Change-Id: I4e7e19e666042c0e8bfdb0ae0bfb2fc8d3ffa565


[ROCm/clr commit: bf88980e0a]
2023-09-15 11:46:48 -04:00
kjayapra-amd 22bc3d52a3 SWDEV-417244 - Create Unique File Desc Store and guarantee no duplicates fds are opened.
Change-Id: I7be7fee52b673f0b1b3facdfbd847b57f2a47cde


[ROCm/clr commit: 85b645731c]
2023-09-13 17:03:18 -04:00
Jaydeep Patel 5b450d5551 SWDEV-418038 - Drop GPU_ENABLE_WAVE32_MODE from RTC.
Change-Id: Iac11f26714e8b3bae14cbf69933ef7c8c8be47da


[ROCm/clr commit: a37c95d7ed]
2023-09-08 02:13:41 -04:00
Anusha GodavarthySurya f464a6ade6 SWDEV-301667 - Optimize performance when graph has single branch
Three for loops iterate over all graph nodes for UpdateStream, FillCommands and
EnqueueCommands has performance drop for large graphs.

Change-Id: I077accf3a4680d5d944b73200fd6498a7a48f25c


[ROCm/clr commit: 530dc6de2a]
2023-09-07 23:35:36 -04:00
Ioannis Assiouras a0ee7e2784 SWDEV-419996 - Allow both kernelParams and extra arguments to be set to null
When kernel function expects no parameters no error should be returned
if both kernelParams and extra arguments are set to null.

Change-Id: I5941bcc400b6fb380e623bdae0233ae3e4f73815


[ROCm/clr commit: 315082e554]
2023-09-07 12:57:46 -04:00
German 5d9912f48b SWDEV-407533 - [ABI Break]Remove Wavelimiter
Change-Id: I6a2f6fb5a0c3acea93fa0200a69679783e76f5bd


[ROCm/clr commit: 7be3a5e33e]
2023-09-07 09:58:41 -04:00
David Salinas 4963cb0b77 SWDEV-419396 - hipcc.bin.exe and hipconfig.bin.exe missing from build
Correct HIPAMD cmake file for finding/instaling hipcc.bin

Change-Id: I3aa56331615fa81a489464210a9be734e917aa47


[ROCm/clr commit: e1efdfbca1]
2023-09-06 10:55:54 -04:00
Ioannis Assiouras 0066c6cb6b SWDEV-420222 - Removed implementation of hipMemcpyArray functions
hipMemcpyArrayToArray, hipMemcpyFromArrayAsync, and hipMemcpyToArrayAsync
are deprecated in cuda and are missing the headers in hip_runtime_api.h.
Removed their implementation from hip_memory.cpp.

Change-Id: I9720aec6241515c56c66b7e90a37b2ed53347eb2


[ROCm/clr commit: 2bc6661737]
2023-09-04 13:35:08 +01:00
Rahul Garg 87bbe33acd SWDEV-418360 - Continue parsing modules even when some module don't have
right binaries built for current device

Change-Id: Icc6a4233fbcede9b2dc6feb78e6bfbd761684c7f


[ROCm/clr commit: c9cf3bdc16]
2023-08-31 14:54:59 -04:00
Ioannis Assiouras f28fa0277e SWDEV-415937 - Make _IMPORT_PREFIX in hip*targets.cmake point to a relative path
Change-Id: Ib0f4321f2954254d0486d741d057f182cb2481a7


[ROCm/clr commit: 209525d6e4]
2023-08-31 08:10:50 -04:00
kjayapra-amd 76cc68ff80 SWDEV-381625 - Parse compiler and linker options from environment variable.
Change-Id: Id5a012b678e5973c4b64dff84444a909aefae006


[ROCm/clr commit: 6a0f80a03d]
2023-08-29 20:24:27 -04:00
Jaydeep Patel 6258f8254f SWDEV-375596 - Device context should not be changed while graph exec update for graph nodes other than empty and host node.
Change-Id: I89d734b111aae5b042386175d2786ce9002771b9


[ROCm/clr commit: d2655d84fd]
2023-08-27 22:58:32 -04:00
Jatin Chaudhary 98b3f79d45 SWDEV-418230 - fix warning seen in HIP headers
This PR fixes warning seen on HIP headers due to -Wignored-attributes.
The warning is attributes for a variable must precede definition.
This also fixes a potential issue with C-style header where templates
were declared outside __cplusplus.

Change-Id: I78bfd391717c7891afb442ef79812ea630c0ff49


[ROCm/clr commit: 8fe5100d16]
2023-08-24 08:41:08 -04:00
Saleel Kudchadker d7a63b9d66 SWDEV-301667 - Port optimization to save extra packet to graphs
Change-Id: Ibaf64a4efe070c42620e6e153c1862a4a0b15664


[ROCm/clr commit: e1e5d071ba]
2023-08-23 16:58:21 -04:00
Jatin Chaudhary 105212ef57 SWDEV-414425 - __half2's member variable should be __half instead of unsigned short
We currently have __half2 made up of unsigned short instead of __half.
This prevents users to do operation seamlessly when they want to operate on individual components.

Change-Id: I856917db905f68055fdf484f526707fe8ea3117d


[ROCm/clr commit: 19afdf719e]
2023-08-22 04:25:19 -04:00
Satyanvesh Dittakavi bee336d360 SWDEV-416443 - hipPointerGetAttributes should return correct type for managed memory
Change-Id: Ic197cd8c9d3f5405616ed6e4924ed5577e636b94


[ROCm/clr commit: 84eae1f0a9]
2023-08-21 07:47:32 -04:00
Vikram 5588dc0583 SWDEV-417558 - Fix dynamic linker error caused by SWDEV-378651 fix
Seems the windows linker error seen with https://gerrit-git.amd.com/c/compute/ec/clr/+/886078
also exists for linux, but only appears with dynamic linker. This fixes both usecases.

Change-Id: I1bb6df151eb1e09f75af4d461ead28bcbaa5f236


[ROCm/clr commit: 62464ca4c3]
2023-08-18 02:21:14 -04:00
Anusha GodavarthySurya b25939b4de SWDEV-415772, SWDEV-414682 - Fix childgraph node execution
Change-Id: If9ffc08d98a57b8daa5f131f72ef1bf2317f29e1


[ROCm/clr commit: f76a40c26d]
2023-08-18 00:45:00 -04:00
David Salinas 8130c99cdc Correct HIPAMD cmake file to install hipcc.bin
Change-Id: Ie90dddbcebba29d4c06cf1485581c9742dd1ad70


[ROCm/clr commit: b00e6fe89e]
2023-08-15 11:51:02 -04:00
Vikram 41ee2ee689 SWDEV-378651 - add proper wavefrontsize link time option to hipRTC, in accordance with env variable GPU_ENABLE_WAVE32_MODE
This is a copy of http://gerrit-git.amd.com/c/compute/ec/hipamd/+/841299
Raising this here again since hipamd repo is frozen.

Change-Id: I8722ef55f78a9176e131fd5766fb11101b51f1b5


[ROCm/clr commit: cec579c006]
2023-08-15 00:12:31 -04:00
taosang2 c4bc05f0d0 SWDEV-408843 - Fix vulkan_interop failure
Fix runtime issues found in  vulkan_interop test

Change-Id: I32c9bed861ddf4fe1d7bba21dce9bd720168c399


[ROCm/clr commit: d2cfb86ddc]
2023-08-11 10:13:56 -04:00
kjayapra-amd 73facd3425 SWDEV-416262 - Adding missing AMD headers on hip files.
Change-Id: I45531004e57c664df5ce4275a49f07ebbad08b7f


[ROCm/clr commit: f2c07d9bc2]
2023-08-11 10:00:23 -04:00
taosang2 088704abeb SWDEV-415029 - [ABI Break] Remove hcc symbols
Change-Id: Ic0082d3960aadbb7ac559141b6e84bd29a75b5cd


[ROCm/clr commit: 051e1005f4]
2023-08-10 21:21:01 -04:00
kjayapra-amd 6b628eca2e SWDEV-416218 - Set the image mapped flag correctly on COMGR path.
Change-Id: I6c0908731f10c8ff5b3e159c0cfb68ce096c7bdf


[ROCm/clr commit: d18f4b1ad4]
2023-08-10 15:52:30 -04:00
Satyanvesh Dittakavi c97dd090f0 SWDEV-415439 - Address segfault issues with hiprtcLinkCreate
Change-Id: I5c5898a9d0afadc344ae2fafc371e9ed647cec6e


[ROCm/clr commit: 8ee985a67b]
2023-08-10 08:28:11 -04:00