Commit-Graf

1398 Incheckningar

Upphovsman SHA1 Meddelande Datum
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
Anusha GodavarthySurya dcad465a22 SWDEV-282361 - HIP support for NVRTC
Change-Id: I82869af8194b595f9a2fb64ad034630786189335


[ROCm/clr commit: c23586440b]
2021-04-20 09:28:58 -07:00
Tao Sang fe7d103d56 SWDEV-279657 - Fix hipMallocManaged-N256M failure
Add concurrentManagedAccess detection in hipMallocManaged test.
Skip test when device doesn't support concurrentManagedAccess.

Change-Id: Ie54046feef3baba857a7068972ec1fc1a60c2dfd


[ROCm/clr commit: 20fd6b8a66]
2021-04-20 09:07:31 -04:00
Sourabh Betigeri eedde26cc9 SWDEV-256723 - Added group partitioning feature in ROCm CG.
Change-Id: Ie54046feef3baba857a7068972ec1fc0a60c2df9


[ROCm/clr commit: 0a0b026304]
2021-04-19 18:53:17 -04:00
Julia Jiang e103d4f31d SWDEV-270961 - Update hip_programming_guide.md for event handling
Change-Id: Ieadac9972e5ee13c05ccb42a679866f494f96f47


[ROCm/clr commit: cb22874ebd]
2021-04-16 12:14:25 -04:00
Satyanvesh Dittakavi 74cf3b8795 SWDEV-281504 - Rename structure names to use reserved names in HIP headers
HIP headers use few structure names as X, Y, and Z. This causes
compilation issues when the apps use similar names as macros.
Renamed the struct names to use reserved names such as
__X, __Y and __Z

Change-Id: I59416c3734f274e853c87d4856b7e616f6cee5f5


[ROCm/clr commit: 009543ec7a]
2021-04-15 09:52:58 -04:00
Tao Sang 73df8d8dd9 SWDEV-273138 - Rearrange device attributes
Change-Id: Iab5902c9a2702456fbe437fdefc40541c48abb74


[ROCm/clr commit: 2c0b63059b]
2021-04-12 17:05:27 -04:00
kjayapra-amd 693c5653c5 SWDEV-274276 - Implement system scope atomics to _system builtins. Default atomics will map to agent.
Change-Id: I63b13063274418e96d4be0159c779127b166bea5
(cherry picked from commit 7c4ae8ca1daac0b75ac36c4e4a45b8d13f219d14)


[ROCm/clr commit: 61d1eaa522]
2021-04-09 10:23:32 -04:00
Sarbojit Sarkar 9d490550c5 SWDEV-260454 - Fix for idenfying bad streams
Change-Id: I122ff6f47535c3c76ab56ba49ab1450ef886b15f


[ROCm/clr commit: daf0cbca3c]
2021-04-07 12:13:30 -04:00
Sarbojit Sarkar 4e5bf6268b SWDEV-280131 - Fix __half2 member access bug
Change-Id: Ic11750d18e4ba47446a7e494c3089a19cb4df783


[ROCm/clr commit: 9cbb283771]
2021-04-07 12:12:02 -04:00
pghafari 4578277e13 SWDEV-245532 - HIP - Vulkan interop
Change-Id: Iba1ef8112e318b4f099da5a4a4602e0dae7de9e3


[ROCm/clr commit: a9304f6111]
2021-03-31 10:23:31 -04:00
Sarbojit Sarkar 47a6267c7c SWDEV-277926 - Updated deprecated APIs in Cuda
Change-Id: I9ff655af227b245067eb760325c395bb562696ee


[ROCm/clr commit: b7a03695c3]
2021-03-29 01:19:19 -04:00
Satyanvesh Dittakavi 85ca63f256 SWDEV-277152 - Add hipMemcpy2DToArrayAsync API in headers
Also, address few scenarios for hipMemcpy2DToArray/Async to return
proper error types

Change-Id: Idbadf666a5e7bebc0f3ea8b7048b79208e04cf6b


[ROCm/clr commit: 68abfb4aff]
2021-03-27 13:50:38 -04:00
jujiang 88c0959afb SWDEV-277423 - Correct hipStreamWaitValue doxygen format
Change-Id: I8914c14cb7a05d5d0bdfa054af14765c872c70a6


[ROCm/clr commit: cc69e95c1a]
2021-03-19 14:10:41 -04:00