5b08779b25
SWDEV-307407 - Add hiprtc's type traits function to match implementation of libcxx
...
Change-Id: I0a10eca329f817bbe31bdc47869b2de104d12d38
2021-12-02 23:32:23 -05:00
e90cb3b07b
SWDEV-305766 - Added new debug APIs to get build information
...
Change-Id: Ibbf0c010cd8f7e6e659f2c4ba932cc8436574431
2021-12-02 12:20:51 -05:00
a6bf18791e
SWDEV-240808 - Added nvidia handling for few graph APIs
...
Change-Id: I8edee87ea75d80152418f76cc8a521b2ba58f139
2021-11-22 07:17:34 -08:00
17cc99c05d
SWDEV-306947 Enable hipAddressModeBorder
...
Enable hipAddressModeBorder.
Fix default of height of hipMallocArray().
Some code improvement.
Change-Id: I57045118e7adf915074c547cbe76349a4cfd72d8
2021-10-27 10:05:53 -04:00
1c51d82dd5
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
2021-10-05 07:44:54 -07:00
1111468b49
SWDEV-240806 - Added few more Graph APIs
...
Change-Id: I028a1fdf30232b0c47443685e03d7ca410d2a0d0
2021-10-05 07:37:11 -04:00
4cd4d2d280
SWDEV-304552 - Add default to return the last error value
...
Change-Id: Ia399033e30aaa454a454067f5afc6f7d1e5ff8dd
2021-10-04 07:23:10 -04:00
70e1fb6a5b
SWDEV-304076 - Fix for Cuda build error
...
Change-Id: Ibca63a08b8d6d1235b51a06c0bc024cd284cee97
2021-09-27 23:55:52 -04:00
7aaad05910
SWDEV-298667 - fix stream operation for Cuda
...
Change-Id: Ida91712e678e324b54293ba48dfca442be390783
2021-09-21 15:07:15 -04:00
673c2deed1
SWDEV-302147 - fix __hip_ds_permutef device function to return float
...
Change-Id: Ie452e90a7f7410401df4a66de468ad850403953c
2021-09-14 02:15:53 -04:00
b25e6d3716
SWDEV-301330 - Remove the hard coded driver version on HIP CUDA platform
...
Change-Id: I0eb10781acc7524174c7ae6fc552c824b7c94b0a
2021-09-02 09:03:04 +00:00
feed2de479
SWDEV-293749 - Add cast before calling the builtin
...
Change-Id: I6224a3693f91a5b4e040bd76918ab04a56a6454b
2021-08-24 10:35:52 -04:00
06e1e4f0de
SWDEV-296918 - Adding unsafe atomic add operation for float and double type
...
Change-Id: I98eabb7412f604733a999bf5e89c2c80b91cfbb1
2021-08-14 12:22:53 +05:30
8a4ca88477
SWDEV-297689 - Moving the vendor specific builtin function calls to hip_cooperative_helper.h header file
...
Change-Id: I797bdde8fbb01285dfda0eac0f960ded260beb8e
2021-08-02 19:14:42 -04:00
ec39f62ee1
SWDEV-297563 - Move surface types
...
Change-Id: Ie2393fb32a30a76c39c81ce17497fa3b131a85b1
2021-08-02 18:48:15 +00:00
3dd9dbb359
SWDEV-297563 - Move declarations to hip
...
Change-Id: Ifdab79945ea2e625e8cef5cd71d638552e9a740b
2021-08-02 11:56:08 -04:00
a71f54d9e9
SWDEV-240806 - Added API hipGraphAddMemcpyNode1D, hipGraphAddEmptyNode, hipGraphExecKernelNodeSetParams
...
Change-Id: I0d7ec8c0ea1abc3fc0f1e10fa7865f355d9cf2ad
2021-07-28 00:09:16 -04:00
c3ca1faee7
SWDEV-292547 - hipStreamPerThread support
...
Change-Id: Id621ce073b0fee9eac03c59ffb78b197fda4ddb5
2021-07-26 20:51:51 -04:00
203c4b9b35
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
2021-07-26 11:30:22 -04:00
cbbf627662
SWDEV-292523 - [hipamd]Change in the signature of streamOperations APIs, particularly 'value' arg to unsigned 'value'
...
Change-Id: I7e31508622865b9986c886c4218ba394ffe9cf9e
2021-07-22 16:24:27 -04:00
9a510f1cf1
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
2021-07-20 20:12:21 -07:00
a8e0ab621e
SWDEV-282289 - Use preprocessor directive for atomicAdd to support backward compatibility.
...
Change-Id: I73f058040afaa782bf6a491b8761a040fbd5b571
2021-07-19 10:46:01 -04:00
e0ae326f4a
SWDEV-294588 - Enable NV printf DTests
...
Add hipLimitPrintfFifoSize.
Add hipDeviceSetLimit(hipLimit_t limit, size_t value) for NV.
Change-Id: Ife884e0c3081b317bdadc8bec7814d1d7c60153a
2021-07-15 11:02:13 -04:00
ff8c20c092
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
2021-07-15 05:41:51 -04:00
e5cbfa8ca9
SWDEV-240807 - Added Implementation for few more graph APIs
...
Change-Id: I76336a22233a208a3f54ff9e90f0c5bf4a1bddb4
2021-07-14 20:56:36 -07:00
4aab5c29ff
SWDEV-278500 - Implement missing atomic APIs and types to match CUDA.
...
Change-Id: I5f5bd94af9b68853bf354c8f90da217434934ddd
2021-07-13 22:15:57 -04:00
14019c2833
SWDEV-293583 - Correct a typo in hipStreamAttachMemAsync
...
Change-Id: I69eb4d126e36a783603e6097fc2faab661dc63cb
2021-07-12 13:14:09 -04:00
68289d1dfe
Revert "SWDEV-293408 Add atomicInc_system and atomicDec_system"
...
This reverts commit 45205c5e53
2021-07-09 13:47:39 -04:00
d9d9e81acb
SWDEV-293742 - Update copyrights end year for hipamd
...
Change-Id: I08f620f84563a9214b59f1b943ed091b67229eab
2021-07-09 12:08:39 -04:00
d208afcb36
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
2021-07-09 11:17:09 -04:00
e5a1f25424
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
2021-07-08 12:49:04 -04:00
45205c5e53
SWDEV-293408 Add atomicInc_system and atomicDec_system
...
- Also revise the implementation of atomicInc/atomicDec based on clang
builtins.
Change-Id: Ia5e06e88c7be1da5f8fc7ac70037a120c604e343
2021-07-08 11:42:16 -04:00
52bc5d7d1f
SWDEV-240806 - hipGraph support for nvidia path
...
Change-Id: Idb51b3ed7ca65474afac0dc714c9097294d46bd2
2021-07-07 06:51:21 -04:00
1e35b26108
SWDEV-234709 - SWDEV-258907 - Reimplement assert() using the new fprintf_stderr facility
...
This reverts commit 18234e1d24
2021-07-07 00:57:36 -07:00
67be27c184
SWDEV-293541 - Update copyright for external reference
...
Change-Id: I0e7522d24313c1974ff4936c81df3159794ea953
2021-07-06 12:56:39 -04:00
19a30de0a6
SWDEV-245414 - fix nvcc CI breakage
...
Change-Id: I34ff533f34cfc2f60abefc0d8f6c6d8266d30f61
2021-06-26 13:31:10 +05:30
7e3c17c023
SWDEV-284435 - StreamOps mapping with cuda drv API
...
Change-Id: I6ed9196cfe59d9004338206f6dd8d6fb367b3ffa
2021-06-25 12:20:40 -04:00
f4680d98a9
SWDEV-285388 - Bring back the inline asm till we have a proper compiler support
...
Change-Id: Ibafe33dd8298f6e19f8b6a6d2aa220b633b76862
2021-06-21 09:15:34 -04:00
a9b4df0ad0
SWDEV-285388 - Allow fallback to asm when builtin not available
...
Change-Id: Ifeee7f3ad1be9ce9b79cf26008b75102153143a5
2021-06-17 21:21:19 -07:00
3fa21c1d49
SWDEV-285388 - Clean up llvm intrinsics using __asm
...
Instead of using inline asm, use clang builtins
for llvm intrinsics.
Change-Id: I30287f5a8de035ccd7e48d10e559a8a2e1d389f7
2021-06-16 13:20:44 -04:00
2223a508f5
SWDEV-290993 - Fix error seen in __launch_bounds__ seen with -Werror -Wpedantic
...
Change-Id: If89c681a5e383c30a9233a183db282787e2f0081
2021-06-15 00:36:35 -07:00
de150e1803
SWDEV-290704 - update hiprtc header with doxygen
...
Change-Id: I93b7ddd2a89f8a214bca7e67bd5b88f6144b70dd
2021-06-14 15:28:32 -04:00
7866ba9713
SWDEV-290278 - typedef for hiprtcResult
...
Change-Id: I93f637dd04ce31aee8ef0ba097f1232af9af8d2b
2021-06-11 11:52:38 -04:00
1936678084
SWDEV-290704 - Add doxygen in hiprtc
...
Change-Id: Ib1efb6874472601c0f45fc5c7f85a01e69b0a958
2021-06-10 17:21:25 -04:00
19c84bc604
ROCMOPS-1956 - Push restructured code to hipamd
...
hipamd will have AMD's ROCCLR based HIP backend implementation
Change-Id: Id7de9634519b4ce46fca71a1b61f3d5b1e3fc459
2021-06-07 21:42:44 +00:00
260a1fed06
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
2021-06-07 00:07:24 +00:00
2b3a4e711b
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
2021-06-02 16:16:14 -04:00
3212fdf4d6
SWDEV-288361 - Implement funnel shift operators
...
Change-Id: I0c73809366f2d21e75f98fdeac7fed0c7591ee34
2021-06-01 11:10:11 -04:00
0e11c59272
SWDEV-240804 - Fix typos in the comments
...
Change-Id: Ic1385daf1e685772b02a11d43fb13f6cde74c4b7
2021-05-29 00:31:46 -04:00
414c80644b
SWDEV-283266 - Workaround RTC macro in vector types
...
Temporarily disable __HIPCC_RTC__ in hip_vector_types.h
while the upstream clang headers are outdated on mainline.
Once upstream patch has landed in mainline, revert this
change. This is a workaround for hiprtc testing.
Change-Id: Ib2cf6023b71431bbfbe3c699076caa4f90f7170c
2021-05-21 15:53:59 +00:00
cjatin
anusha GodavarthySurya
Tao Sang
Sarbojit Sarkar
Satyanvesh Dittakavi
Sourabh Betigeri
Rahul Garg
Christophe Paquot
kjayapra-amd
Aaron Enye Shi
German Andryeyev
Michael LIAO
agunashe
Maneesh Gupta
Julia Jiang
Joseph Greathouse