a8fde39f74
SWDEV-311744 - Update floating point max/min atomic implementation
...
Clang builtins doesnt yet support max/min atomics with float/double
parameters, Hence modify atomicMax/Min to use compare and swap
implementation
Change-Id: Ia351f9b136129fe25f0eddcbbb17549553247182
[ROCm/clr commit: f3c5f12d26
2021-12-07 13:29:44 -05:00
68c75c9fb7
SWDEV-303204 - Disable texture/image Apis on some devices
...
If the target device doesn't support image,
compiler will send out unavailable error if device texture apis
are called; and host texture apis will return hipErrorNotSupported.
Remove useless include/hip/amd_detail/texture_functions.h.
Add hipDeviceAttributeImageSupport attribute to check image
support in runtime.
Add __HIP_NO_IMAGE_SUPPORT(=1) macro in device code to indicate
texture apis not supported.
Change-Id: Ia891493e681a61980a2444859a90e046a9ebea39
[ROCm/clr commit: 5acc8b5102
2021-12-04 08:14:08 -05:00
6c68d56c17
SWDEV-309292 - add hipPos definition in CUDA path
...
Change-Id: Ia81d5db77d7403cafb583fda8083d0f4dbe33835
[ROCm/clr commit: 69117705c8
2021-12-04 04:40:34 -05:00
2982b73c91
SWDEV-307407 - Add hiprtc's type traits function to match implementation of libcxx
...
Change-Id: I0a10eca329f817bbe31bdc47869b2de104d12d38
[ROCm/clr commit: 5b08779b25
2021-12-02 23:32:23 -05:00
7cac13e36e
SWDEV-305766 - Added new debug APIs to get build information
...
Change-Id: Ibbf0c010cd8f7e6e659f2c4ba932cc8436574431
[ROCm/clr commit: e90cb3b07b
2021-12-02 12:20:51 -05:00
1d922d6d57
SWDEV-240808 - Added nvidia handling for few graph APIs
...
Change-Id: I8edee87ea75d80152418f76cc8a521b2ba58f139
[ROCm/clr commit: a6bf18791e
2021-11-22 07:17:34 -08:00
f970a1be0f
SWDEV-306947 Enable hipAddressModeBorder
...
Enable hipAddressModeBorder.
Fix default of height of hipMallocArray().
Some code improvement.
Change-Id: I57045118e7adf915074c547cbe76349a4cfd72d8
[ROCm/clr commit: 17cc99c05d
2021-10-27 10:05:53 -04:00
78f89618cb
SWDEV-240806 - Added few Graph API Implementation
...
hipGraph APIs clone, childGraph, RemoveDependencies, GetEdges,GetDependencies, GetDependentNodes, GetType and DestroyNode
hipStream APIs GetCaptureInfo, GetCaptureInfo_v2, UpdateCaptureDependencies.
Change-Id: Ib0f4cb8ea335698eecdd6d744ffab1e954153673
[ROCm/clr commit: 1c51d82dd5
2021-10-05 07:44:54 -07:00
ea786b1810
SWDEV-240806 - Added few more Graph APIs
...
Change-Id: I028a1fdf30232b0c47443685e03d7ca410d2a0d0
[ROCm/clr commit: 1111468b49
2021-10-05 07:37:11 -04:00
257bb9d2fc
SWDEV-304552 - Add default to return the last error value
...
Change-Id: Ia399033e30aaa454a454067f5afc6f7d1e5ff8dd
[ROCm/clr commit: 4cd4d2d280
2021-10-04 07:23:10 -04:00
2e1449e9af
SWDEV-304076 - Fix for Cuda build error
...
Change-Id: Ibca63a08b8d6d1235b51a06c0bc024cd284cee97
[ROCm/clr commit: 70e1fb6a5b
2021-09-27 23:55:52 -04:00
b97595d514
SWDEV-298667 - fix stream operation for Cuda
...
Change-Id: Ida91712e678e324b54293ba48dfca442be390783
[ROCm/clr commit: 7aaad05910
2021-09-21 15:07:15 -04:00
e7a40bf6f6
SWDEV-302147 - fix __hip_ds_permutef device function to return float
...
Change-Id: Ie452e90a7f7410401df4a66de468ad850403953c
[ROCm/clr commit: 673c2deed1
2021-09-14 02:15:53 -04:00
5bfa893ac8
SWDEV-301330 - Remove the hard coded driver version on HIP CUDA platform
...
Change-Id: I0eb10781acc7524174c7ae6fc552c824b7c94b0a
[ROCm/clr commit: b25e6d3716
2021-09-02 09:03:04 +00:00
7b095ace14
SWDEV-293749 - Add cast before calling the builtin
...
Change-Id: I6224a3693f91a5b4e040bd76918ab04a56a6454b
[ROCm/clr commit: feed2de479
2021-08-24 10:35:52 -04:00
d898f71794
SWDEV-296918 - Adding unsafe atomic add operation for float and double type
...
Change-Id: I98eabb7412f604733a999bf5e89c2c80b91cfbb1
[ROCm/clr commit: 06e1e4f0de
2021-08-14 12:22:53 +05:30
1cbb056f4c
SWDEV-297689 - Moving the vendor specific builtin function calls to hip_cooperative_helper.h header file
...
Change-Id: I797bdde8fbb01285dfda0eac0f960ded260beb8e
[ROCm/clr commit: 8a4ca88477
2021-08-02 19:14:42 -04:00
ab2cc17a2e
SWDEV-297563 - Move surface types
...
Change-Id: Ie2393fb32a30a76c39c81ce17497fa3b131a85b1
[ROCm/clr commit: ec39f62ee1
2021-08-02 18:48:15 +00:00
62a018191f
SWDEV-297563 - Move declarations to hip
...
Change-Id: Ifdab79945ea2e625e8cef5cd71d638552e9a740b
[ROCm/clr commit: 3dd9dbb359
2021-08-02 11:56:08 -04:00
f25a9e8217
SWDEV-240806 - Added API hipGraphAddMemcpyNode1D, hipGraphAddEmptyNode, hipGraphExecKernelNodeSetParams
...
Change-Id: I0d7ec8c0ea1abc3fc0f1e10fa7865f355d9cf2ad
[ROCm/clr commit: a71f54d9e9
2021-07-28 00:09:16 -04:00
597831dd66
SWDEV-292547 - hipStreamPerThread support
...
Change-Id: Id621ce073b0fee9eac03c59ffb78b197fda4ddb5
[ROCm/clr commit: c3ca1faee7
2021-07-26 20:51:51 -04:00
f97143a0d9
SWDEV-294594 - Fix hipPointerGetAttributes test on NV
...
Replace return value of hipPointerGetAttributes() on NV from
hipErrorUnknown to hipErrorInvalidValue if memory has been freed.
Change-Id: I3fe6dbc35a7a14aa9109df297b7885df83d28149
[ROCm/clr commit: 203c4b9b35
2021-07-26 11:30:22 -04:00
c396ebad94
SWDEV-292523 - [hipamd]Change in the signature of streamOperations APIs, particularly 'value' arg to unsigned 'value'
...
Change-Id: I7e31508622865b9986c886c4218ba394ffe9cf9e
[ROCm/clr commit: cbbf627662
2021-07-22 16:24:27 -04:00
f9116b4328
SWDEV-281658 - Preserve the callback IDs enum ordering
...
Use continue instead of break to make sure we process the
whole hip_runtime_api.h file.
Change-Id: Ied2a8df69ed9eb1dc04d6b2d0d7b117ce2a2b6b3
[ROCm/clr commit: 9a510f1cf1
2021-07-20 20:12:21 -07:00
d579eb9104
SWDEV-282289 - Use preprocessor directive for atomicAdd to support backward compatibility.
...
Change-Id: I73f058040afaa782bf6a491b8761a040fbd5b571
[ROCm/clr commit: a8e0ab621e
2021-07-19 10:46:01 -04:00
2fe45ab575
SWDEV-294588 - Enable NV printf DTests
...
Add hipLimitPrintfFifoSize.
Add hipDeviceSetLimit(hipLimit_t limit, size_t value) for NV.
Change-Id: Ife884e0c3081b317bdadc8bec7814d1d7c60153a
[ROCm/clr commit: e0ae326f4a
2021-07-15 11:02:13 -04:00
20f48d91aa
SWDEV-294395 - HIPRTC add definitions for amd_hip_vector_types.h
...
Add typedefs for int32 and int64. Add templates provided in
system headers such as type_traits used in our HIP header
amd_hip_vector_types.h. Make replacements for clang builtin,
__is_convertible_to.
Change-Id: I4129b3f4f37238e2dda5b64d55e5cffe4d4480c6
[ROCm/clr commit: ff8c20c092
2021-07-15 05:41:51 -04:00
5464d40940
SWDEV-240807 - Added Implementation for few more graph APIs
...
Change-Id: I76336a22233a208a3f54ff9e90f0c5bf4a1bddb4
[ROCm/clr commit: e5cbfa8ca9
2021-07-14 20:56:36 -07:00
2b5806542f
SWDEV-278500 - Implement missing atomic APIs and types to match CUDA.
...
Change-Id: I5f5bd94af9b68853bf354c8f90da217434934ddd
[ROCm/clr commit: 4aab5c29ff
2021-07-13 22:15:57 -04:00
43c91585b5
SWDEV-293583 - Correct a typo in hipStreamAttachMemAsync
...
Change-Id: I69eb4d126e36a783603e6097fc2faab661dc63cb
[ROCm/clr commit: 14019c2833
2021-07-12 13:14:09 -04:00
4528b90f85
Revert "SWDEV-293408 Add atomicInc_system and atomicDec_system"
...
This reverts commit 5ea09794fc68289d1dfe
2021-07-09 13:47:39 -04:00
fae697b4d6
SWDEV-293742 - Update copyrights end year for hipamd
...
Change-Id: I08f620f84563a9214b59f1b943ed091b67229eab
[ROCm/clr commit: d9d9e81acb
2021-07-09 12:08:39 -04:00
e3a6104868
SWDEV-281658 - Preserve the callback IDs enum ordering
...
This change addresses the rocprofiler and HIP backward compatibility
issues. Before this patch, each time the hip_prof_str.h header was
generated, the ordering of the callbacks IDs changed, causing
incompatibilities between tools compiled with the old header and
runtimes compiled with the new headers (or vice versa).
To make the API callback IDs stable, the previous version of the header
is read to extract the enum values so that the same values can be
assigned in the new header.
Also, to make diffing different versions of the hip_prof_str.h easier
to read, all other sections (types, macros, helper functions) are now
alphabetically ordered.
If an update to the checked-in hip_prof_str.h file is required, the
cmake build is aborted and a message printed on stderr. The build will
not be successful until the checked-in hip_prof_str.h and the generated
hip_prof_str.h match.
Change-Id: I38b920e601185f7365a76a6584df91a7e8a11798
[ROCm/clr commit: d208afcb36
2021-07-09 11:17:09 -04:00
5555c7eed9
SWDEV-284682 - Revert Workaround RTC macro in vector types
...
Re-enable __HIPCC_RTC__ in hip_vector_types.h which require
an upstream clang patch, 6823af0ca858b54e09e5be61a19d067ccd0bd6b7.
Once upstream patch has landed in mainline, merge this for
hiprtc functionality.
Change-Id: Ife884e0c3081b307bdadc8bec7804d1d7c60153b
[ROCm/clr commit: e5a1f25424
2021-07-08 12:49:04 -04:00
5ea09794fc
SWDEV-293408 Add atomicInc_system and atomicDec_system
...
- Also revise the implementation of atomicInc/atomicDec based on clang
builtins.
Change-Id: Ia5e06e88c7be1da5f8fc7ac70037a120c604e343
[ROCm/clr commit: 45205c5e53
2021-07-08 11:42:16 -04:00
58cbab41ef
SWDEV-240806 - hipGraph support for nvidia path
...
Change-Id: Idb51b3ed7ca65474afac0dc714c9097294d46bd2
[ROCm/clr commit: 52bc5d7d1f
2021-07-07 06:51:21 -04:00
c2268df391
SWDEV-234709 - SWDEV-258907 - Reimplement assert() using the new fprintf_stderr facility
...
This reverts commit 125de2dbe61e35b26108
2021-07-07 00:57:36 -07:00
f808c4e28a
SWDEV-293541 - Update copyright for external reference
...
Change-Id: I0e7522d24313c1974ff4936c81df3159794ea953
[ROCm/clr commit: 67be27c184
2021-07-06 12:56:39 -04:00
52dd6c20c9
SWDEV-245414 - fix nvcc CI breakage
...
Change-Id: I34ff533f34cfc2f60abefc0d8f6c6d8266d30f61
[ROCm/clr commit: 19a30de0a6
2021-06-26 13:31:10 +05:30
b99ebf8d00
SWDEV-284435 - StreamOps mapping with cuda drv API
...
Change-Id: I6ed9196cfe59d9004338206f6dd8d6fb367b3ffa
[ROCm/clr commit: 7e3c17c023
2021-06-25 12:20:40 -04:00
adc4c3aabe
SWDEV-285388 - Bring back the inline asm till we have a proper compiler support
...
Change-Id: Ibafe33dd8298f6e19f8b6a6d2aa220b633b76862
[ROCm/clr commit: f4680d98a9
2021-06-21 09:15:34 -04:00
06e2a2a59d
SWDEV-285388 - Allow fallback to asm when builtin not available
...
Change-Id: Ifeee7f3ad1be9ce9b79cf26008b75102153143a5
[ROCm/clr commit: a9b4df0ad0
2021-06-17 21:21:19 -07:00
a785d554ae
SWDEV-285388 - Clean up llvm intrinsics using __asm
...
Instead of using inline asm, use clang builtins
for llvm intrinsics.
Change-Id: I30287f5a8de035ccd7e48d10e559a8a2e1d389f7
[ROCm/clr commit: 3fa21c1d49
2021-06-16 13:20:44 -04:00
1b23aa0d88
SWDEV-290993 - Fix error seen in __launch_bounds__ seen with -Werror -Wpedantic
...
Change-Id: If89c681a5e383c30a9233a183db282787e2f0081
[ROCm/clr commit: 2223a508f5
2021-06-15 00:36:35 -07:00
060408115c
SWDEV-290704 - update hiprtc header with doxygen
...
Change-Id: I93b7ddd2a89f8a214bca7e67bd5b88f6144b70dd
[ROCm/clr commit: de150e1803
2021-06-14 15:28:32 -04:00
e8ff063910
SWDEV-290278 - typedef for hiprtcResult
...
Change-Id: I93f637dd04ce31aee8ef0ba097f1232af9af8d2b
[ROCm/clr commit: 7866ba9713
2021-06-11 11:52:38 -04:00
e3253b830d
SWDEV-290704 - Add doxygen in hiprtc
...
Change-Id: Ib1efb6874472601c0f45fc5c7f85a01e69b0a958
[ROCm/clr commit: 1936678084
2021-06-10 17:21:25 -04:00
dd95d3d23c
ROCMOPS-1956 - Push restructured code to hipamd
...
hipamd will have AMD's ROCCLR based HIP backend implementation
Change-Id: Id7de9634519b4ce46fca71a1b61f3d5b1e3fc459
[ROCm/clr commit: 19c84bc604
2021-06-07 21:42:44 +00:00
28f8d08148
SWDEV-288707 - Merge HIP refactored code to staging
...
These changes move-
- rocclr based implementation inside src/hipamd/src
- platform specific (both nvidia and amd) headers inside
src/hipamd/include/hip
Change-Id: Ia29791a727244952591fe1d813dcef0303b73a9e
[ROCm/clr commit: 260a1fed06
2021-06-07 00:07:24 +00:00
a073c62d95
SWDEV-240804 - Add hipMemAdvise() extension
...
Add coarse grain memory extension. The new advice will allow HMM
to disable cache coherency policy to improve performance
Change-Id: I3c792d6a96896b983a7ffccddaa0ded06d183212
[ROCm/clr commit: 2b3a4e711b
2021-06-02 16:16:14 -04:00
Satyanvesh Dittakavi
Tao Sang
haoyuan2
cjatin
anusha GodavarthySurya
Sarbojit Sarkar
Sourabh Betigeri
Rahul Garg
Christophe Paquot
kjayapra-amd
Aaron Enye Shi
German Andryeyev
Michael LIAO
agunashe
Maneesh Gupta
Julia Jiang