ee124dda09
SWDEV-508540 - fix the max blocks per multiprocessor calculation ( #737 )
2025-08-11 10:17:18 +05:30
4646a756d9
SWDEV-542218 - Remove attribute(aligned) from ext_vector_type as it i… ( #802 )
...
SWDEV-542218 - Remove attribute(aligned) from ext_vector_type as it is iignored
2025-08-08 13:09:56 +01:00
9b045922a8
SWDEV-538195 - Introduce threshold for handler submission ( #723 )
...
- When doing device/stream sync, we can submit a handler which may
introduce some host side delays. Use DEBUG_CLR_BATCH_CPU_SYNC_SIZE to
batch commands for host wait. Default for HIP is 8 commands.
- Investigation is underway in ROCr but need to address this for now in
HIP runtime.
2025-08-06 20:34:42 -07:00
7e777d3755
SWDEV-534394 - Kernel launch stream check ( #533 )
...
hipErrorInvalidResourceHandle is returned if stream is not on the launching device
2025-08-05 10:39:37 -07:00
111f12cbed
SWDEV-546137 - Don't rely on __cplusplus under hiprtc environment ( #806 )
2025-08-04 21:33:26 +02:00
f094d16157
SWDEV-533754 - Fixed mem leak in capturing gpu packets ( #365 )
2025-08-04 14:58:04 +01:00
2a02d2c2f3
SWDEV-545273 - Respect HIP_LAUNCH_PARAM_BUFFER_SIZE ( #770 )
2025-08-03 17:32:52 -07:00
2da49283c8
Fix undefined symbol at runtime with newer versions of LLVM ( #791 )
2025-08-01 08:15:02 -07:00
c329b548eb
SWDEV-541799 - Return hipSuccess from hipFreeAsync if ptr to free is … ( #683 )
...
SWDEV-541799 - Return hipSuccess from hipFreeAsync if ptr to free is nullptr to match with hipFree.
2025-08-01 14:41:40 +05:30
76d2c4135e
SWDEV-543350 - restrictions on usage of hipMemcpyWithStream ( #727 )
...
* SWDEV-543350 - Do not hipMemcpyWithStream to be called during stream capture
* update comment
---------
Co-authored-by: Jatin Chaudhary <jatchaud@amd.com >
2025-08-01 14:41:02 +05:30
3f6f9d6081
SWDEV-539710 - Defer allocation of managed variable ( #652 )
...
Co-authored-by: Rahul Manocha <rmanocha@amd.com >
2025-07-31 08:30:23 -07:00
c88f345229
SWDEV-532824 - Fixed log_printf errors for codeql ( #427 )
...
Co-authored-by: Jimbo Xie <jiabaxie@amd.com >
2025-07-31 08:17:41 -07:00
3bbc8bd170
SWDEV-540733 - Add PCI CHIP ID device attribute ( #647 )
...
SWDEV-540733 - Add PCI CHIP ID Device Attribute
Co-authored-by: Rahul Manocha <rmanocha@amd.com >
2025-07-30 19:43:07 -07:00
2c6ec7df45
SWDEV-534207 - fix use of uninitialized variable at hipEventRecord_common() ( #771 )
2025-07-23 16:49:12 +05:30
5fc6208b19
SWDEV-533964 - use __builtin_readcyclecounter() only in clock64 ( #368 )
2025-07-22 10:41:23 +05:30
b15c1657b8
SWDEV-502579 - Remove duplicated symbols ( #21 )
...
Remove duplicated compiler symbols from hip-rt. hip-rt should use symbols such as EF_AMDGPU_MACH_AMDGCN_XXX and
ELFABIVERSION_AMDGPU_HSA_VX defined in compiler header.
2025-07-22 10:41:01 +05:30
c43ee71e96
SWDEV-542905 - Update the appropriate grid size in capture hipExtModuleLaunchKernel ( #740 )
2025-07-21 13:57:15 +05:30
9cd8757717
SWDEV-523483 - Update atomics add-operation in CLR ( #751 )
2025-07-19 06:48:54 +05:30
1edac1bf3a
SWDEV-537486 - Change the SPIRV bundle entry id to match 4-field triple ( #513 )
2025-07-17 09:29:51 +05:30
0313e20706
SWDEV-540629 - Update the current device ID ( #699 )
2025-07-15 21:40:26 +05:30
918b0bdb7a
SWDEV-542832 - Refactor vector types alignment ( #713 )
2025-07-15 21:09:31 +05:30
397f303d97
SWDEV-508776 - support VGPRs validation ( #274 )
...
Clarify some VGPRs terms description.
Fix some wrong query logics of availableVGPRs_ and
availableRegistersPerCU_ in device info.
Add hipDeviceAttributeMaxAvailableVgprsPerThread
attribute query.
Remove hardcoding of following
info_.vgprAllocGranularity_
info_.vgprsPerSimd_
2025-07-09 10:46:52 -04:00
71c6535b07
SWDEV-536367 - Make DEPRECATED message in roc-obj tools STDERR ( #469 )
2025-07-09 17:01:33 +05:30
32e027e66c
SWDEV-540609 - hipGraph capture of hipExtModuleLaunchKernel assumed grid size was a multiple of block size ( #694 )
2025-07-09 16:05:40 +05:30
81238db679
SWDEV-515426 - Remove HIP_USE_RUNTIME_UNBUNDLER ( #205 )
...
* remove HIP_USE_RUNTIME_UNBUNDLER
* clang-format
* Generic to use comgr
* Remove HIP_ALWAYS_USE_NEW_COMGR_UNBUNDLING_ACTION flag
* Removes runtime unbundling unused and debug Code
* Removes stale functions
2025-07-08 21:45:31 +05:30
21f6842fff
SWDEV-536925 - Check for C++ compiler instead of C when building hip ( #490 )
...
Change cmake to use CMAKE_CXX_COMPILER_ID since CMAKE_COMPILER_IS_GNUCC is deprecated
2025-07-01 12:59:54 -07:00
a7d7687b8f
SWDEV-539145 - Support extended fine grained system memory pool ( #603 )
...
* Add hipHostMalloc() new flag hipHostMallocUncached which will force to allocate pinned
host memory on extended fine grained system memory pool.
* Add hipHostAlloc() new flag hipHostAllocUncached which will force to allocate pinned
host memory on extended fine grained system memory pool.
* Add hipHostRegister() new flag hipHostRegisterUncached which will force to map
host memory onto extended fine grained system momory pool.
2025-07-01 10:10:10 +05:30
5e77c58bd0
SWDEV-536813 - Make alignment 16 for special cases ( #609 )
2025-06-27 14:20:16 +05:30
a2dafbeacf
SWDEV-531400_SYMLINK remove SYMLINK ( #525 )
...
Co-authored-by: Jonathan Luu <jonatluu@amd.com >
2025-06-26 15:53:39 -04:00
c64d56195f
SWDEV-531400 - Remove file reorganization backward compatibility (clr hip) ( #472 )
...
* SWDEV-531400 Remove file reorganization backward compatibility (clr hip)
* SWDEV-531400 remove backwards compatibility for opencl
* SWDEV-531400 remove header_template.hpp.in
---------
Co-authored-by: Jonathan Luu <jonatluu@amd.com >
2025-06-26 15:53:11 -04:00
a4631b5700
SWDEV-533232 Add num_threads API in cooperative_groups ( #437 )
...
* Add num_threads API in cooperative_groups
* Reimplementsize API as its alias.
* Update changelog
2025-06-26 15:05:17 +05:30
349b83c1f6
SWDEV-512344 - Allow unmapping of only complete subbuffers ( #608 )
...
* Do not allow partial unmapping
* Add check to prevent out of bounds unmap
* Improve code quality
* Use getOrigin instead of getOffset
2025-06-26 15:01:33 +05:30
5d53c83806
SWDEV-535490 - Improve logging ( #441 )
...
- Include HIP version/githash in the logs
- Add a new method to print library path
2025-06-24 13:00:00 -07:00
7755660eeb
SWDEV-533964 - Let comgr compile SPIRV to exec directly ( #494 )
2025-06-23 09:59:53 -04:00
0635f13d9a
SWDEV-526498 - [HIPCC] Stop including perl scripts in hipcc packages ( #474 )
2025-06-23 18:23:54 +05:30
49690b8b38
Fix rocWMMA specialization ( #532 )
...
Co-authored-by: Aidan Belton <abeltons@amd.com >
2025-06-23 18:22:37 +05:30
3faece02dc
SWDEV-536813 - Fix HIP_vector_base alignment ( #501 )
...
* SWDEV-536813 - Fix HIP_vector_base alignment
Change-Id: I6ee211437768bbdf42186bcd0805b8c2290373da
* Remove alignas for vec3
Change-Id: If93c55327cad38cf179bdd2a89faa725b0a0fc15
* align array to match native_vector
Change-Id: I54fbdba01c19241a4c4945ba4c35ac6d40f17ea6
* update
Change-Id: Ib7de5a7ebde0b2a5c18fe5c70f7329a90807abfb
2025-06-23 18:21:51 +05:30
428fce9fd6
SWDEV-519446 Part 2: Update unsafe atomic function file header ( #394 )
...
* SWDEV-519446 Part 2: Update unsafe atomic function file header
* Use __HIP_ATOMICS_IGNORE_DENORMAL_MODE to denote [[clang::atomic(ignore_denormal_mode)]] when condition met.
2025-06-19 19:12:59 +05:30
adda2602e1
SWDEV-535738 - Properly define size_t for windows ( #481 )
2025-06-18 19:32:11 +05:30
e88d9fabe0
SWDEV-537656 - Added c++11 include guard for constexpr HIP_vector_type operator== ( #517 )
2025-06-13 12:05:41 +05:30
0877d257e6
SWDEV-510589 - fix libgcc1 dependency on Debian 10 ( #252 )
...
* fix libgcc1 should added to HIP_RUNTIME_DEB_STDPKG_DEPENDENCIES and not HIP_RUNTIME_RPM_STDPKG_DEPENDENCIES
* add libgcc1 and not libgcc_s1 also to HIP_RUNTIME_RPM_STDPKG_DEPENDENCIES as it seems rpms are also generated when compiling on Debian
2025-06-12 14:22:28 +05:30
67f6409eb1
SWDEV-519446 - Part 1: update normal atomic function file header ( #345 )
...
Remove the scope of __has_builtin(__hip_atomic_compare_exchange_strong) == false
2025-06-12 09:16:51 +05:30
b7778ecd65
SWDEV-537139 - Add missing typename qualifier to permuteType ( #505 )
2025-06-11 08:03:10 +05:30
10ea744996
SWDEV-511020 - fix bugs in surface function header ( #449 )
2025-06-11 08:00:42 +05:30
543925e048
SWDEV-529899 - [ABI Break] remove unnamed namespace from fp16 operations ( #244 )
...
Change-Id: I4feb9089b4cee145300dc78fc43a4f42473f5b1c
2025-06-06 21:22:37 +05:30
a01134a1ab
SWDEV-536048 - Add explicit cast to int when warpSize is used with == operator ( #473 )
2025-06-06 12:22:31 +05:30
1bce89ca51
SWDEV-535738 - Use the type traits implementation from __hip_internal namespace in hip headers ( #471 )
2025-06-05 00:14:56 +05:30
c2f6c98006
Add HIP_vector_base constructor ( #456 )
...
Change-Id: I57571f6bf9876d3a9ff312b952858527ec6abc7b
2025-06-03 12:23:38 +05:30
54a2e943d7
SWDEV-535184 - Fix to switch HIP_RUNTIME_API_TABLE_STEP_VERSION 9 and 10 ( #448 )
2025-06-02 21:24:40 +05:30
a018d4278a
SWDEV-535738 - Use __hip_internal instead of std namespace for device code. ( #455 )
2025-06-02 20:09:17 +05:30
Chaudhary, Jatin Jaikishan
Assiouras, Ioannis
Kudchadker, Saleel
Xie, Pengda
Brzak, Branislav
Betigeri, Sourabh
Sumner, Brian
Patel, Jaydeepkumar
Manocha, Rahul
Xie, Jiabao(Jimbo)
Hernandez, Gerardo
Sang, Tao
Dittakavi, Satyanvesh
Jiang, Julia
Salinas, David
Belton-Schure, Aidan
Luu, Jonathan
Sicarov, Dragoslav
Arandjelovic, Marko