AI/rocm-systems
2
0
Форкнуть 0
Код Задачи Запросы на слияние Действия Пакеты Проекты Релизы Вики Активность
6 587 коммитов 3 Ветки 0 Теги
e8c5a72cff4e4e5bd887b9f6fe882462c0a67cae
Граф коммитов

31 Коммитов

Автор SHA1 Сообщение Дата
TomSang 3fd16c0b5b SWDEV-266829 - Enable more tests on AMD and NV devices (#2336) 
* SWDEV-266829 - Enable more tests on AMD and NV devices

1. Enable tests on AMD and NV devices
  tests/src/runtimeApi/event/hipEventMultiThreaded.cpp
    Loops and threads per core are changed smaller so that test can
    finish in a shorter time.
  tests/src/runtimeApi/stream/hipStreamCreateWithPriority.cpp
    Fix logic error on how to get priority_normal

2. Simply enable test on AMD device
  tests/src/runtimeApi/memory/hipManagedKeyword.cpp
  tests/src/runtimeApi/module/hipManagedKeyword.cpp
  tests/src/runtimeApi/stream/hipStreamACb_MultiThread.cpp
  tests/src/runtimeApi/memory/p2p_copy_coherency.cpp

3. Simply enable test on NV device
 tests/src/runtimeApi/module/hipModuleLoadDataMultThreaded.cpp

4. Fix typo
  tests/src/runtimeApi/stream/hipStreamAddCallbackCatch.cpp

5. Remove useless tests
 tests/src/hipC.c
 tests/src/hipHcc.cpp

Change-Id: Ia4406353e64d69bd34c58ebb56185701f7ce1caa

* Remove tests/src/runtimeApi/module/hipModuleLoadDataMultThreaded.cpp for cuda test

Co-authored-by: anusha GodavarthySurya <Anusha.GodavarthySurya@amd.com>
Co-authored-by: Jenkins <jenkins-compute@amd.com>
 2021-09-14 13:36:32 +05:30
Tao Sang ec7e25b7e0 SWDEV-294591 - Fix hipEventIpc failure on NV 
Remove unnecessary codes

Change-Id: I4248b2cebd3dd156f9d5d427e1897da22fb964ec
 2021-07-29 10:16:07 -04:00
Tao Sang c053d60282 SWDEV-294591 - Fix hipEventIpc failure on NV 
make hipIpcOpenEventHandle has the same behavour of cudaIpcOpenEventHandle.
Add Api usages.

Change-Id: I4248b2cebd3de156f9d5d427e1797da22fb964eb
 2021-07-28 15:28:39 -04:00
agunashe d529637fbc SWDEV-293742 - Update copyright end year 
Change-Id: I2cb7bbd9a6d9da28116ba9dd9cec4e60525444e2
 2021-07-07 12:57:23 -04:00
Satyanvesh Dittakavi f300d11931 SWDEV-278464 - Update unit test hipEventMultiThreaded 
Run with multiple threads to catch possible race condition
Disable running the test by default on CI as this takes lot of time

Change-Id: I1c1a66fd5c72f8d2bf7ad120461384488b46abbd
 2021-05-21 02:57:14 -04:00
Satyanvesh Dittakavi 98d1acf1f2 SWDEV-278464 - Unit Test For Suspected race condition 
Change-Id: I561ec3073a6e6813c5f7aa50983fcf098c6ac54a
 2021-04-29 23:40:43 -04:00
Rahul Garg f2c96993e1 SWDEV-229520 - Reenable hipEventIpc test 
Change-Id: Ib40fb07a07cc447182e23664573c5e37a1194a32
 2021-04-21 13:55:15 -04:00
Sourabh Betigeri 8f67e24cbd SWDEV-274727 - Disabling tests temporarily 
Change-Id: I695daebe15f592afdfee8e4efe4d8966b6e9922a
 2021-03-30 13:02:19 -04:00
Sourabh Betigeri 4223d3ecb4 SWDEV-274727 - The callback associated with the event was being processed after the event is destroyed. Commit after resolving merge conflict. 
Change-Id: Ia7383c83318ca0c2a4f21f7aaf22b1cebd828cf0
 2021-03-18 15:08:58 -04:00
Tao Sang 38b0c952a6 SWDEV-273943 - Enable runtimeApi.event dtest 
Add device_id_ in hip::event to match cuda behaviour in
hipEventQuery() and hipEventRecord().
Enable hipEventElapsedTime test on AMD platform.
Workarround sporadic crash of hipEventIpc test due to
some bug of event ipc.
Add missing hipEventDestroy() in some event tests.
Fix some logic code errors.
Fix typo in comment.

Change-Id: I9ec74c475161b3e31df48d193449023e921f2924
 2021-03-16 17:12:08 -04:00
DURGESH KROTTAPALLI 44753583e7 SWDEV-238517 - Enhancing hip unit tests 
[dtest] Tests for hipEvent related APIs

Added Negative scenarios for hipEvent related APIs

1. Verifying all hipEvent related APIs by passing nullptr.
2. Pass illegal/unknown flag to hipEventCreateWithFlags API

Change-Id: Ia0a24065d16fe0f5ee28a88e280c25c1be0c3590
 2021-02-24 06:29:26 -05:00
Tao Sang ce4ba590fe SWDEV-272088 - Fix runtimeApi/event/hipEventElapsedTime issue 
runtimeApi/event/hipEventElapsedTime will report invalid resource error
on cuda due to wrong calling sequence. The fix will arrange the calling
in right sequence.

Change-Id: I3db28a962888566ea135e3cbdefa68d373e2d369
 2021-02-23 12:36:40 -05:00
Rahul Garg c307baf3da Add IPC Events support 
Change-Id: Iac2bf3d5e1d9a993bebbb066c20d300d6f05558b
 2021-01-08 20:09:26 +00:00
Tao Sang c2adc70d4d 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
 2021-01-05 10:39:31 -05:00
agodavar d10124e1d7 cmake hip-rocclr as default build,change HIP_PLATFORM to amd|nvidia 
Change-Id: I59d2e15b297b6ca2d5eee1a6dee642bdb01a3839
 2020-10-21 07:26:14 -04:00
Payam c5f76c3de3 name change vdi to rocclr 
Change-Id: I06d198bbb4a499e153b290b73a92afed3553b252
 2020-05-06 09:14:30 -04:00
root 2689246de6 Merge master into amd-master-next 
Change-Id: I3fc1dc0c860d627053537581e75561e8a7efe327
 2020-04-26 22:19:37 +00:00
Maneesh Gupta a0b5dfd625 Merge in the rocclr based hip runtime (#2032) 
* Merge master-next changes in master (include vdi development in master branch)
 2020-04-23 09:12:06 -07:00
Jeff Daily ef596cd088 add IPC event support (#1996) 2020-04-17 10:31:22 +05:30
Sarbojit2019 b80a2c3966 hipEventElapsedTime should respect device (#1992) 
Fixes SWDEV-228636.
Also added a unit test to verify this.
 2020-04-06 15:38:25 +05:30
Evgeny Mankov 4921678b6c [HIP] Clean-up deprecated HIP error codes 
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle
 2019-12-23 17:01:35 +03:00
Maneesh Gupta 9f2d1453fb [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED 
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074
 2019-05-09 09:59:18 +05:30
Maneesh Gupta 52e320f396 Replace hipLaunchKernel -> hipLaunchKernelGGL 
Change-Id: I4d99009e1199811d417becf1e1b934ec4d4e30be
 2018-10-17 14:32:25 +05:30
Saleel Kudchadker 1daee67eb6 Fix record_event and hipStreamSync2 tests. The test should expect null stream to complete if synchrionize is called as per the spec 2018-08-31 12:54:23 -07:00
Maneesh Gupta 1ba06f63c4 Apply .clangformat to all repo source files 
Change-Id: I7e79c6058f0303f9a98911e3b7dd2e8596079344
 2018-03-12 11:29:03 +05:30
Alex Voicu c2482d1255 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. 2017-11-01 15:09:59 +00:00
Rahul Garg 4b98572f47 Enable hipStreamSync2 and record_event dtests 2017-08-24 15:51:58 +05:30
Maneesh Gupta b3a9e202b1 [dt] temporarily disable broken tests 
Change-Id: I3ce23e410dc36e06d460263d768412f8368a6699
 2017-07-18 11:17:02 +05:30
Ben Sander 39c18e5e5f 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
 2017-06-05 08:50:22 -05:00
Ben Sander 8ce6d17983 Update tests. 
Fix some NVCC issues.
Add hipStreamSync2, record_event tests.
 2017-06-04 20:18:37 -05:00
Aditya Atluri 5e3d63c0a3 changed __global__ attribute 
1. Moved around tests and added them to HIT

Change-Id: I5d75280c42a5af852670ebabc7305ee56721ec7b
 2017-02-03 10:53:36 -06:00