Commit Graph

1411 Commits

Author SHA1 Message Date
Satyanvesh Dittakavi 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
Jatin Chaudhary 7b095ace14 SWDEV-293749 - Add cast before calling the builtin
Change-Id: I6224a3693f91a5b4e040bd76918ab04a56a6454b


[ROCm/clr commit: feed2de479]
2021-08-24 10:35:52 -04:00
cjatin 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
Sourabh Betigeri 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
Rahul Garg ab2cc17a2e SWDEV-297563 - Move surface types
Change-Id: Ie2393fb32a30a76c39c81ce17497fa3b131a85b1


[ROCm/clr commit: ec39f62ee1]
2021-08-02 18:48:15 +00:00
Rahul Garg 62a018191f SWDEV-297563 - Move declarations to hip
Change-Id: Ifdab79945ea2e625e8cef5cd71d638552e9a740b


[ROCm/clr commit: 3dd9dbb359]
2021-08-02 11:56:08 -04:00
Anusha GodavarthySurya f25a9e8217 SWDEV-240806 - Added API hipGraphAddMemcpyNode1D, hipGraphAddEmptyNode, hipGraphExecKernelNodeSetParams
Change-Id: I0d7ec8c0ea1abc3fc0f1e10fa7865f355d9cf2ad


[ROCm/clr commit: a71f54d9e9]
2021-07-28 00:09:16 -04:00
Sarbojit Sarkar 597831dd66 SWDEV-292547 - hipStreamPerThread support
Change-Id: Id621ce073b0fee9eac03c59ffb78b197fda4ddb5


[ROCm/clr commit: c3ca1faee7]
2021-07-26 20:51:51 -04:00
Tao Sang 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
Sourabh Betigeri 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
Christophe Paquot 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
kjayapra-amd 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
Tao Sang 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
Aaron Enye Shi 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
Anusha GodavarthySurya 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
kjayapra-amd 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
German Andryeyev 43c91585b5 SWDEV-293583 - Correct a typo in hipStreamAttachMemAsync
Change-Id: I69eb4d126e36a783603e6097fc2faab661dc63cb


[ROCm/clr commit: 14019c2833]
2021-07-12 13:14:09 -04:00
Michael LIAO 4528b90f85 Revert "SWDEV-293408 Add atomicInc_system and atomicDec_system"
This reverts commit 5ea09794fc.

Change-Id: I808b52758cc08882daa7fc889e53ca4c2fe64a61


[ROCm/clr commit: 68289d1dfe]
2021-07-09 13:47:39 -04:00
agunashe fae697b4d6 SWDEV-293742 - Update copyrights end year for hipamd
Change-Id: I08f620f84563a9214b59f1b943ed091b67229eab


[ROCm/clr commit: d9d9e81acb]
2021-07-09 12:08:39 -04:00
Christophe Paquot 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
Aaron En Ye Shi 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
Michael LIAO 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
Anusha GodavarthySurya 58cbab41ef SWDEV-240806 - hipGraph support for nvidia path
Change-Id: Idb51b3ed7ca65474afac0dc714c9097294d46bd2


[ROCm/clr commit: 52bc5d7d1f]
2021-07-07 06:51:21 -04:00
Maneesh Gupta c2268df391 SWDEV-234709 - SWDEV-258907 - Reimplement assert() using the new fprintf_stderr facility
This reverts commit 125de2dbe6.

Change-Id: Ic1bbf4e4e6f950934d9ba02224ef61a96bdd0e9b


[ROCm/clr commit: 1e35b26108]
2021-07-07 00:57:36 -07:00
Rahul Garg f808c4e28a SWDEV-293541 - Update copyright for external reference
Change-Id: I0e7522d24313c1974ff4936c81df3159794ea953


[ROCm/clr commit: 67be27c184]
2021-07-06 12:56:39 -04:00
Jatin 52dd6c20c9 SWDEV-245414 - fix nvcc CI breakage
Change-Id: I34ff533f34cfc2f60abefc0d8f6c6d8266d30f61


[ROCm/clr commit: 19a30de0a6]
2021-06-26 13:31:10 +05:30
Sarbojit Sarkar b99ebf8d00 SWDEV-284435 - StreamOps mapping with cuda drv API
Change-Id: I6ed9196cfe59d9004338206f6dd8d6fb367b3ffa


[ROCm/clr commit: 7e3c17c023]
2021-06-25 12:20:40 -04:00
Maneesh Gupta 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
Maneesh Gupta 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
Aaron En Ye Shi 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
Jatin Chaudhary 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
Julia Jiang 060408115c SWDEV-290704 - update hiprtc header with doxygen
Change-Id: I93b7ddd2a89f8a214bca7e67bd5b88f6144b70dd


[ROCm/clr commit: de150e1803]
2021-06-14 15:28:32 -04:00
Sarbojit Sarkar e8ff063910 SWDEV-290278 - typedef for hiprtcResult
Change-Id: I93f637dd04ce31aee8ef0ba097f1232af9af8d2b


[ROCm/clr commit: 7866ba9713]
2021-06-11 11:52:38 -04:00
Julia Jiang e3253b830d SWDEV-290704 - Add doxygen in hiprtc
Change-Id: Ib1efb6874472601c0f45fc5c7f85a01e69b0a958


[ROCm/clr commit: 1936678084]
2021-06-10 17:21:25 -04:00
Rahul Garg 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
Rahul Garg 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
German Andryeyev 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
Joseph Greathouse 5037dd6a4c SWDEV-288361 - Implement funnel shift operators
Change-Id: I0c73809366f2d21e75f98fdeac7fed0c7591ee34


[ROCm/clr commit: 3212fdf4d6]
2021-06-01 11:10:11 -04:00
German Andryeyev d100715c28 SWDEV-240804 - Fix typos in the comments
Change-Id: Ic1385daf1e685772b02a11d43fb13f6cde74c4b7


[ROCm/clr commit: 0e11c59272]
2021-05-29 00:31:46 -04:00
Aaron En Ye Shi c9f19b9d26 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


[ROCm/clr commit: 414c80644b]
2021-05-21 15:53:59 +00:00
Tao Sang fad72a437f SWDEV-282588 - Improve clock64()
Let clock64() read s_memtime to prevent rolling over
Add wall_clock64() to read s_memrealtime

Change-Id: I706387355add75852c570be2656131ef99e8968f


[ROCm/clr commit: 26235f49e6]
2021-05-17 13:19:04 -04:00
Aaron En Ye Shi 3a23df8893 SWDEV-263959 - Fix device decl with long and llong
Windows may expect long and ulong to be 4 bytes, while
Linux expects 8 bytes. Instead, use uint64_t for
unsigned long, and unsigned long long, and use int64_t
for long and long long to be consistent.

Change-Id: I6ed1cdde43721bcaaab0245644d607b1adbf9884


[ROCm/clr commit: dd643ec517]
2021-05-14 11:59:27 -04:00
pghafari f0e63eb72f SWDEV-245532 - HIP - Vulkan interop semaphores
Change-Id: I89be5ee84d4728d76e1987d5016c944c0dbc9a96


[ROCm/clr commit: ccff5216f0]
2021-05-11 11:44:59 -04:00
Aaron En Ye Shi 3d40b92eeb SWDEV-283266 - __HIPCC_RTC__ macro added to HIP headers
For hipRTC on Windows, add macro __HIPCC_RTC__ to allow
online compilation of with device functions excluding standard
C/C++ headers, system headers, and host HIP APIs.

Change-Id: I1d91f042baf1359856ec83ab7030dc58785e0334


[ROCm/clr commit: 688693e9fd]
2021-05-10 17:28:07 +00:00
Anusha Godavarthy Surya 1fe1fe9361 SWDEV-240806 - Initial commit for hipGraph and stream capture infrastructure
On StreamBegincapture captures the parameters passed to APIs and respective node will be created and added to graph
All parameters are passed to STREAM_CAPTURE macro, it checks if stream in capture mode and redirects the call to the capture function and returns
Updated hipStream and hipEvent with capture parameters
Added handling for hipStreamBeginCapture & hipStreamEndCapture

Change-Id: Ic8926a7b4336c2cc81f0b3a9a224aa392c474134


[ROCm/clr commit: 8cc0e04239]
2021-05-07 17:38:16 -04:00
Anusha GodavarthySurya 766c6fbdcb SWDEV-271978 - Function __byte_perm to match CUDA behavior
Selector indices are as follows (the upper 16-bits of the selector are not used): selector[0] = s<2:0> selector[1] = s<6:4> selector[2] = s<10:8> selector[3] = s<14:12>

Change-Id: Ibf76c6ec2374f1f5b9bba8bd9dbd73660f830eea


[ROCm/clr commit: e9cc056d25]
2021-05-05 03:00:32 -04:00
kjayapra-amd d3ff861a37 SWDEV-245533 - Implementing Mipmap array APIs
Change-Id: I222c8d0fcbd50cdefd702462e689463bb36366d2


[ROCm/clr commit: 31d412c292]
2021-04-30 16:33:43 -04:00
Satyanvesh Dittakavi 9e4b7ff5bb SWDEV-283388 - Fix hipMemRangeGetAttributes on Nvidia Platform
Change-Id: I5daeacd9dd5c6ce7f914d6e6e45dd41fb2a675a5
hipMemRangeGetAttributes was returning hipErrorInvalidValue due to improper
mapping of the arguments to cudaMemRangeGetAttributes.


[ROCm/clr commit: cc39ceab25]
2021-04-29 06:06:03 -04:00
Satyanvesh Dittakavi 59c118bb57 SWDEV-281789 - Add missing HMM attributes on CUDA path
Change-Id: I11167eea006301e01a1f91708bf6d0ac832d8b7f


[ROCm/clr commit: 120436423c]
2021-04-26 13:54:01 -04:00
Yaxun (Sam) Liu e04783afe7 SWDEV-255234 - remove workaround for warpSize after clang fix is released
The workaround is no longer needed as the compiler emits the macro itself.

Change-Id: I6a06e73353628bcea71f6bd23503ab6d8e42a29d


[ROCm/clr commit: 37b90c2f64]
2021-04-26 08:49:15 -04:00