AI/rocm-systems
2
0 Форкнуть 0
Код Задачи Запросы на слияние Действия Пакеты Проекты Релизы Вики Активность
6 098 коммитов 3 Ветки 0 Теги
d33b577c95406ad51f105a86d8338b939d0aa98e
Граф коммитов
71 Коммитов
Автор SHA1 Сообщение Дата
agunashe a4ff63a29b SWDEV-293742 - Update copyright end year 
Change-Id: I2cb7bbd9a6d9da28116ba9dd9cec4e60525444e2


[ROCm/hip commit: d529637fbc]
 2021-07-07 12:57:23 -04:00
Satyanvesh Dittakavi 7a49cdb7a0 SWDEV-292618 - Enable/Fix few of the dtests on Nvidia Platform 
Change-Id: I6f4e37b293aac9054a768f9d692b914f52d42756


[ROCm/hip commit: 57569c62f4]
 2021-06-30 01:23:29 -04:00
Satyanvesh Dittakavi a951797224 SWDEV-286830 - Fix hipStreamACb_ThrdBehaviour on windows 
use sleep_for which works cross-platform
for other tests as well

Change-Id: I915444d620e9fad0b9eda93bcdd244f9956ab8d5


[ROCm/hip commit: 03ae7251de]
 2021-05-24 03:18:36 -04:00
Aaron En Ye Shi 34625c7a88 SWDEV-283930 - Fix bugs in HIP Tests on Windows 
Windows doesn't have headers unistd.h, sys/wait.h, so
remove them for _WIN64. Also, Windows doesn't have rand_r
so define it. Fixes builds for HIP tests:
d2dMemCpyWithPinnedHostMemory, hipMemset3DFunctional,
hipModuleLoadMultProcessOnMultGPU,
hipModuleLoadUnloadStress, hipModuleNegative,
hipStreamACb_ThrdBehaviour, hipMemcpyNegativeMThrdMSize,
hipStreamACb_MStrm_Mgpu, StreamAddCallback,
hipStreamACb_StrmSyncTiming, hipStreamACb_MultiCalls,
hipMallocConcurrency, hipMemset3DRegressMultiThread,
and hipSetGetDevice.

Change-Id: Id2f98d664716026c590d879e464ba467d4c071be


[ROCm/hip commit: 9edd31100d]
 2021-04-30 21:38:45 +00:00
cjatin e2d28dbe76 SWDEV-269879 - Adding function that recommends optimal thread count 
Change-Id: I42eb94a058c1b7f9253182e16ff1c3389a836d61


[ROCm/hip commit: 7ba1a0cf72]
 2021-02-09 13:34:08 -05:00
Tao Sang c618b6aeff Remove hip-hcc codes: Part three 
1.Rename include/hip/hcc_detail/ as include/hip/amd_detail/

2.Rename include/hip/nvcc_detail/ as include/hip/nvidia_detail/

3.Create __HIP_PLATFORM_AMD__ to replace __HIP_PLATFORM_HCC__

4.Create __HIP_PLATFORM_NVIDIA__ to replace __HIP_PLATFORM_NVCC__

After hcc_detail, nvcc_detail, __HIP_PLATFORM_HCC__ and __HIP_PLATFORM_NVCC__
have been removed from upstream, they will be removed from hip runtime.

Change-Id: I1ae457effd739d6c25bca203c1724b026be21fce


[ROCm/hip commit: c2adc70d4d]
 2021-01-05 10:39:31 -05:00
Aryan Salmanpour c9443d9a24 [dtest] add a test case for hipExtStreamGetCUMask API 
Change-Id: I2b03f06fc96c4af0c3dcf4efc0b83126971aab46


[ROCm/hip commit: 2d84056764]
 2020-11-20 14:08:02 -05:00
agodavar 13436a7e1f cmake hip-rocclr as default build,change HIP_PLATFORM to amd|nvidia 
Change-Id: I59d2e15b297b6ca2d5eee1a6dee642bdb01a3839


[ROCm/hip commit: d10124e1d7]
 2020-10-21 07:26:14 -04:00
Vladislav Sytchenko e4caaa2a77 Revert "Revert "Merge branch 'amd-master-next' into amd-npi-next"" 
This reverts commit 28b17d3dbd.

Reason for revert: <INSERT REASONING HERE>

Change-Id: I92ceb171e31026ed1864704cef2fc1497b883ef9


[ROCm/hip commit: ad2d55c144]
 2020-10-05 13:20:58 -04:00
Vladislav Sytchenko 28b17d3dbd Revert "Merge branch 'amd-master-next' into amd-npi-next" 
This reverts commit 258d79bca7.

Reason for revert: <INSERT REASONING HERE>

Change-Id: I53322718dadde2c98f96140b8e260ec7ee9ef721


[ROCm/hip commit: 374ead1d19]
 2020-10-05 13:02:39 -04:00
mkumarmi 7f4fd6e62e [dtest] Disable few tests on NVCC platform 
Few of the tests are being validated in nvcc platform.  Till then
these tests are disabled.

SWDEV-238517 for enhancing hip unit tests

Change-Id: I1acbfe90c6ea39f3de676e98f0e3c33cbac97888


[ROCm/hip commit: 5bf2a70382]
 2020-09-18 04:34:00 -04:00
Aryan Salmanpour 2c90a43675 [dtest] disable hipStreamCreateWithPriority test temporarily as it fails randomly on Jenkins 
Change-Id: I4edcd555653ef8e7562245da3a6f310d60884fe0


[ROCm/hip commit: ee149e4610]
 2020-07-30 16:18:04 -04:00
Jatin Chaudhary 2982f07b9c Fixing/Disabling tests on nvcc path 
Change-Id: I7ed4a1246943867482ff595d5f98bb25bd79074b


[ROCm/hip commit: e7eaafe165]
 2020-07-30 00:39:07 -04:00
sushantkumar14 18f347c3c9 [dtest] Added hipStreamGetPriority API test 
SWDEV-238517 for enhancing hip unit tests

Change-Id: Icff175360815ba6e25a6954a67947b65caff3711


[ROCm/hip commit: 77ae61cff7]
 2020-07-09 01:59:44 -04:00
Lakhan singh Thakur 2ac9c18acf [dtest] Enhancing hipStreamAddCallback() api test 
-Scenario-1:: This test case is used to verify if the callback function
              called through  hipStreamAddCallback() api completes the
	      execution in order as hipStreamAddCallback() api queued
	      in their respective streams: hipStreamACb_AltEnqueue.cpp
-Scenario-2:: This test case tests if Host thread continues with next
              command after hipStreamAddCallback() api or wait for
	      callback() call to finish. Ideally Host thread should not
              wait for callback to
              finish: hipStreamACb_ThrdBehaviour.cpp
-Scenario-3:: Streams are launched in individual GPUs with different
              kernel Verify that all the kernels queued are executed
	      before the callback is hit: hipStreamACb_MStrm_Mgpu.cpp
-Scenario-4:: Checks the callback execution in the same order it was
              added. Also, it checks if the number of callbacks
	      executed are same as the number of callbacks added:
	      hipStreamACb_order.cpp
-Scenario-5:: This test case checks whether hipStreamSynchronize() is
              taking less time than the time taken by Callback()
	      function launched by hipStreamAddCallback() api :
	      hipStreamACb_StrmSyncTiming.cpp
-Scenario-6:: This test case is used to check if the runtime is ok when
              hipStreamAddCallback() is called back to back multiple
	      calls: hipStreamACb_MultiCalls.cpp
-Scenario-7:: This test case is used to check the behaviour of HIP when
              multiple hipStreaAddCallback() are called over multiple
	      Threads:hipStreamACb_MultiThread.cpp
              (Currently disabled)

SWDEV-238517 for enhancing hip unit tests

Change-Id: I9c7b7df6766c728b2b201df18726b9fbdd434c06


[ROCm/hip commit: d613d1d58b]
 2020-07-07 00:43:32 -04:00
Christophe Paquot 5a8857b3e9 Do not deferred stream creation now that we multiplex HW queues 
SWDEV-239856

Change-Id: I156650faf832f86891f00ee167269509edd844ec


[ROCm/hip commit: c8f9afa9da]
 2020-06-09 19:16:25 -04:00
Payam dac652e8df Observed softhang while running hipStreamAddCallbackCatch SWDEV-236746 
Workaround hipStream deadlock issue as the same lock was used twice SWDEV-236746

Change-Id: Icc60104ce6edf4cfd2a3a889bab78a6caadd50b7


[ROCm/hip commit: a524f13c97]
 2020-06-04 14:11:22 -04:00
Aryan Salmanpour cddd09b85d [dtest] add a multi stream test for (SWDEV-237846) 
Change-Id: I4a1d764df75af7019d0f38313e5e0a6a224818f8


[ROCm/hip commit: e44d7f578b]
 2020-05-28 23:36:10 -04:00
Aryan Salmanpour 72a611f9e3 [dtest] add a test for hipExtStreamCreateWithCUMask API 
Change-Id: Ib567e559c5ab7d04ac5c300fd7e15eedfc4fb6e6


[ROCm/hip commit: 9b6228f6c9]
 2020-05-26 18:15:09 -04:00
Payam 0c8b343931 name change vdi to rocclr 
Change-Id: I06d198bbb4a499e153b290b73a92afed3553b252


[ROCm/hip commit: c5f76c3de3]
 2020-05-06 09:14:30 -04:00
Maneesh Gupta 4e1f6f2a0e Merge branch 'amd-master' into amd-master-next 
Change-Id: I3094c15008093f2072bcd38aca4ea90aeae2d97b


[ROCm/hip commit: 2af31479e2]
 2020-04-09 06:31:00 -04:00
Evgeny Mankov abef353b5b [HIP] Clean-up deprecated HIP error codes 
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle


[ROCm/hip commit: 4921678b6c]
 2019-12-23 17:01:35 +03:00
Sarbojit2019 6679cd3998 Revert [HIP] Fixed hipStreamAddCallback (#1674) 
This reverts commit fa1e44aa0e.
Addresses SWDEV#212675.

[ROCm/hip commit: 153a959280]
 2019-11-20 11:55:46 +05:30
Sarbojit2019 fa1e44aa0e [HIP] Fixed hipStreamAddCallback [SWDEV#165185] (#1425) 
Fixed hipStreamAddCallback() as requested in SWDEV#165185
Added unit test to test the behavior


[ROCm/hip commit: 45613311d7]
 2019-11-07 13:18:12 +05:30
Maneesh Gupta 7f41814190 [dtests] Fix typo in hipAPIStreamDisable.cpp (#1227) 
Change-Id: Ib88a6be49ba192578129bb88ad09817839981398

[ROCm/hip commit: 8a28afeb84]
 2019-07-17 07:28:38 +00:00
Konstantin Pyzhov 993f323887 Disable hipStreamSync2 test for hip-clang. 
[ROCm/hip commit: 7cbaa5082b]
 2019-05-20 02:13:30 -04:00
Maneesh Gupta fa07d40cdd [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED 
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074


[ROCm/hip commit: 9f2d1453fb]
 2019-05-09 09:59:18 +05:30
Alex Voicu de15c6988d Re-sync with upstream. 
[ROCm/hip commit: fe959f7bd7]
 2018-10-18 12:27:03 +01:00
Maneesh Gupta c4a93adb74 Replace hipLaunchKernel -> hipLaunchKernelGGL 
Change-Id: I4d99009e1199811d417becf1e1b934ec4d4e30be


[ROCm/hip commit: 52e320f396]
 2018-10-17 14:32:25 +05:30
Maneesh Gupta b35590db18 Implementation for stream priority 
- Requires ROCm 1.9.x or higher
- Requires HCC with PR#886 merged

Change-Id: Id7c95ea091ee610e80c9ad815f1cb989cba570ca


[ROCm/hip commit: da64156fb2]
 2018-10-05 16:27:46 +05:30
Alex Voicu 312d29ebaf Align with HC Next. 
[ROCm/hip commit: c6720e882b]
 2018-09-17 11:50:29 +03:00
Maneesh Gupta 4f42ee762d Apply .clangformat to all repo source files 
Change-Id: I7e79c6058f0303f9a98911e3b7dd2e8596079344


[ROCm/hip commit: 1ba06f63c4]
 2018-03-12 11:29:03 +05:30
Maneesh Gupta c1f3d1409c hipStreamAddCallback.cpp: Replace unistd sleep with sleep_for 
Change-Id: I7a5d40a1acd8be76a0f175bcfa731ad89fb88d81


[ROCm/hip commit: e0b91d32dd]
 2018-01-31 10:48:17 +05:30
Maneesh Gupta 1429c44459 Fix hipStreamAddCallback testcase for nvcc 
Change-Id: Ieec4b8d7933d8d68394d21d27132da206111efc8


[ROCm/hip commit: 5bce9ea5ef]
 2018-01-30 12:32:46 +05:30
Maneesh Gupta 02bedf46dc Implement hipStreamAddCallback 
Change-Id: Ib851e4d86ba9c8406ca37b88162ea483ccbc9d36


[ROCm/hip commit: cebb070d30]
 2017-12-19 16:06:14 +05:30
Phaneendr-kumar Lanka f8d610cf61 [nvccWarnings] Fix warnings seen with dtests on nvcc path 
[ROCm/hip commit: eea7d495c7]
 2017-12-14 14:10:37 +05:30
Ben Sander 8ef230eaaf Temporarily disable a couple tests pending some HCC work 
[ROCm/hip commit: 62cbe22d50]
 2017-12-01 21:46:28 +00:00
Alex Voicu 8d51eaafb6 Revert "Revert adoption of CUDA indexing in general - this can only work with later versions of the compiler, just like module based dispatch, and thus must be guarded against usage in earlier (e.g. 1.6) versions." 
This reverts commit 1c50968


[ROCm/hip commit: 32e11e7dc6]
 2017-11-29 21:49:10 +00:00
Alex Voicu fcc42f035e Revert "Revert adoption of CUDA indexing in general - this can only work with later versions of the compiler, just like module based dispatch, and thus must be guarded against usage in earlier (e.g. 1.6) versions." 
This reverts commit d2fd1f5


[ROCm/hip commit: fbaf729f88]
 2017-11-29 21:36:29 +00:00
Alex Voicu 3c936777aa Re-sync with upstream. 
[ROCm/hip commit: c5f2b22d0d]
 2017-11-20 15:34:50 +00:00
Alex Voicu 962bf7bfda This implements the trivial change needed to move back from the hip{Something}_{x, y, z} macros to the natural CUDA syntax of Something.{x, y, z}. This is contained in lines 384-404 in hip_runtime.h. All of the other changes have to do with changing unit tests to use this syntax. The macros are retained for backwards compatibility. 
[ROCm/hip commit: cffd0e14eb]
 2017-11-19 01:54:12 +00:00
Alex Voicu 4950373967 Merge remote-tracking branch 'origin/master' into feature_use_module_based_dispatch_instead_of_pfe 
# Conflicts:
#	tests/src/runtimeApi/stream/hipStreamSync2.cpp


[ROCm/hip commit: 3d248927e4]
 2017-11-08 10:26:30 +00:00
Alex Voicu 35d8af2001 Clean up trailing whitespace so as to reduce noise in #246. 
[ROCm/hip commit: d8e323d4b5]
 2017-11-08 00:08:55 +00:00
Phaneendr-kumar Lanka a8da9c1c3b More tests for memory,stream & error APIs 
[ROCm/hip commit: 093279b10b]
 2017-11-06 11:31:52 +05:30
Alex Voicu 70a41e7dac This switches HIP from its currently convoluted macro + pfe based dispatch mechanism to a more natural one partially based on the existing module API. The basic idea is that HCC will always correctly emit __global__ functions: as empty-bodied stubs, on host, and as kernels, on device. It then becomes trivial to obtain the mangled name on host, at dispatch, from the function's address, and then to use the mangled name to retrieve the kernel. This should address all problems stemming from serialisation, dubious mismatches due to the manufactured functor, macro-isms et al. It also immediately enables support for generalised globals as a consequence of that being available in the module API. Finally, it will make debug much easier, since the actual names of the __global__ functions will automatically be used in traces etc. One detail is that due to how dispatch works now (hipLaunchKernel and hipLaunchKernelGGL are themselves variadic function templates which deduce the function type of the callee), in certain cases it may be necesssary to insert explicit casts to ensure that the variadic argument list selects a viable overload - this can be observed in some unit tests. Eventually we may be able to remove this limitation, but for now it does not appear terribly onerous. The code is not extremely HIPpie, nor is it fully optimised, but rather is intended as a starting point for the HIP team to make its own. 
[ROCm/hip commit: c2482d1255]
 2017-11-01 15:09:59 +00:00
Ben Sander 2a23d6dbe7 Refactor hipStreamWaitEvent 
- Null streams use same flow as non-null.
- Add HIP_SYNC_STREAM_WAIT
- Resolve null stream.


[ROCm/hip commit: 882dab4536]
 2017-08-31 03:00:14 +00:00
Rahul Garg 1d4213af20 Enable hipStreamSync2 and record_event dtests 
[ROCm/hip commit: 4b98572f47]
 2017-08-24 15:51:58 +05:30
Maneesh Gupta 3e230cfcc6 [dt] temporarily disable broken tests 
Change-Id: I3ce23e410dc36e06d460263d768412f8368a6699


[ROCm/hip commit: b3a9e202b1]
 2017-07-18 11:17:02 +05:30
Ben Sander 445042f916 Fix HIP_SYNC_NULL_STREAM=0 mode. 
- Fix null-stream sync
- hipStreamDestroy of null stream returns hipErrorInvalidResourceHandle
- Update documentation.
- Add tests for null stream sync, hipEventElapsedTime.
- Rename internal enum hipEventStatusRecorded to hipEventStatusComplete
- refactor hipStreamWaitEvent to streamline control-flow


[ROCm/hip commit: 39c18e5e5f]
 2017-06-05 08:50:22 -05:00
Ben Sander f3950e0748 Update tests. 
Fix some NVCC issues.
Add hipStreamSync2, record_event tests.


[ROCm/hip commit: 8ce6d17983]
 2017-06-04 20:18:37 -05:00