Commit Graph

105 Commits

Author SHA1 Message Date
ROCm CI Service Account 9ef84113f3 SWDEV-286739 - Support hipDeviceAttributeWallClockRate (#2984)
Part 4: Add unit test of wall_clock64()

Change-Id: I52cbba6d67d21cde6da19c5ab533159f426a9bf7

[ROCm/hip commit: fb938a607f]
2022-10-19 19:12:01 +05:30
ROCm CI Service Account 76c9a958ea SWDEV-341956 - update coordinates in dtest runtimeApi (#2761)
Change-Id: I058afba16452d1831067faf31020c979e5a99fa7


[ROCm/hip commit: 45870b83b2]
2022-06-22 12:06:02 -07:00
ROCm CI Service Account 4a74649360 SWDEV-305992 - Improve texture tests (#2646)
Enable more texture supports for hip-rocclr.
Skip texture tests on device that doesn't support images.
SWDEV-322257 - Fix issues of image tests skipped on
NVidia devices.

Change-Id: Ia99d06b1e97fc945f1b740e47710f4dcd70f38ca


[ROCm/hip commit: 643f8dbd36]
2022-05-09 08:46:20 -07:00
ROCm CI Service Account 8ceb856ec0 SWDEV-324081 - Fix for dtest (#2540)
Change-Id: I114cb00d0bf2f899f1f299891ccbd4c0bea29150

[ROCm/hip commit: 8e2aee5dbe]
2022-03-10 15:03:29 +05:30
TomSang b87ef5aa18 SWDEV-303204 - Disable texture/image Apis on some devices. (#2381)
Modify texture tests to pass on devices that don't support texture.
Add hipDeviceAttributeImageSupport to check image support in runtime

Change-Id: Ia89c494e651a6198a24448b59a91e046a9ebea38

[ROCm/hip commit: 5c8af57480]
2021-12-02 11:46:13 +05:30
Julia Jiang 3351c0a2f7 SWDEV-286322 - clean up trailing space - part2 (#2383)
Change-Id: Id659c029a33874bc9a7d4c42bffd06cdc1845e2e

[ROCm/hip commit: 48b91908bc]
2021-11-25 15:08:06 +05:30
TomSang 3aa91ecfd7 SWDEV-299966 - Enable texture test (#2340)
Enable the following test directed_tests/runtimeApi/module/hipModuleTexture2dDrv --tests 0x14

Change-Id: I98eabb7412f615733a999bf5e89c2c80b91cfbb2

[ROCm/hip commit: b05a0503f1]
2021-10-06 17:23:33 +05:30
Julia Jiang 3d53651d31 SWDEV-286322 - remove unnecessary executable permission (#2362)
Change-Id: Iebcac3f717ed916554d57a4b839d27b0427efd84

[ROCm/hip commit: c61bbcce35]
2021-09-24 16:28:03 +05:30
TomSang f4aa2b9977 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>

[ROCm/hip commit: 3fd16c0b5b]
2021-09-14 13:36:32 +05:30
Julia Jiang eec75aa436 SWDEV-286322 - remove unnecessary executable permission in some HIP files (#2329)
Change-Id: If992963761a73d709e08330bc36f2c979d5dcae9

[ROCm/hip commit: 56d6d27a6f]
2021-09-02 08:47:57 +05:30
arjun-raj-kuppala 361dbfd63a Jenkins pipeline code to enable external ci on develop branch (#2302)
* Create Jenkinsfile
* Temporarily disable hipModuleLoadDataMultThreaded test on nvidia

Change-Id: Id061e8a43cccdf0d944081268758b946d2448a6e

[ROCm/hip commit: 402211e28e]
2021-08-10 10:16:04 +05:30
Tao Sang 1dcac5ba79 SWDEV-294596 - Fix module test failure on NV
Remove unecessary codes

Change-Id: I4248b2cebd3de156f9d5d427e0697da22fb964ea


[ROCm/hip commit: a0b301089c]
2021-07-25 21:21:12 -04:00
Tao Sang 927bc28565 SWDEV-294596 - Fix module test failure on NV
1.Fix hipModuleNegative failure on all NV GPUs
a.Add signal handler for signal sent by cuda functions.
b.Make hipModuleGetGlobal match cuModuleGetGlobal behavour.
That is, if one of the first two parameters is nullptr, ignore it.

2.Fix hipModuleLoadDataMultThreaded failure on NV RTX5000
Improve lamda function.

Change-Id: I3fe6dbc35a7a14aa9119df197b7885df83d28047


[ROCm/hip commit: ae30c5cd6b]
2021-07-23 22:04:19 -04:00
Tao Sang d33b577c95 SWDEV-266829 - Enable more NV DTests
Enable NV DTests as many as possible.

Change-Id: I3fe6dba35a7a140a9a19df197b7885df83d28044


[ROCm/hip commit: 4b5468e8e6]
2021-07-19 11:07:43 -04:00
Tao Sang f985ba8b26 SWDEV-295037 - Fix passed() in DTests
passed() should not call exit(0) which will prevent object
destructor being called.

Change-Id: Ibaee0d85cb616727dc5db557bb9422702670b688


[ROCm/hip commit: c74e2da333]
2021-07-19 10:59:04 -04:00
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 cac5c6a37c SWDEV-292618 - Enable/Fix more dtests on Nvidia Platform
Change-Id: I0fdac4ddefa693674dfce66ba29306f34ad886c9


[ROCm/hip commit: f5703d57cd]
2021-07-07 03:23:42 -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
Tao Sang 5000aa0f9b SWDEV-291011 - Fix ModuleLaunchKernel on NV
Should not add extra for non-parameter dummyKernel()
in hipModuleLaunchKernel()

Change-Id: If6f881ebb027bd3e8435d3de5295b00277e96a6a


[ROCm/hip commit: 87ba31e596]
2021-06-16 11:52:38 -04:00
Anusha GodavarthySurya 878ce92905 SWDEV-255979 - Add support for dynamic __managed__ variables
Change-Id: I62b790853ea3ab3b7ac57bab389046c627fdecce


[ROCm/hip commit: d9fffacfb3]
2021-06-01 05:09:51 -04:00
Tao Sang bed2381766 SWDEV-283515 - Fix crashing in kernel launch on MGPUS
Fix wrong mixing of current device and stream device in
ihipModuleLaunchKernel() and hipLaunchCooperativeKernel().

Fix missing hipSetDevice() in hipMemcpyWithStream* tests.

Change-Id: I09333bb40d239bb42c832df5ea16d17eeaeff5e7


[ROCm/hip commit: a95ff95bf7]
2021-04-29 14:46:47 -04:00
sumanthtg 578ce42bc5 SWDEV-278967 - Changes to handle dtest failures on cuda runtime version 11.2
Change-Id: I79c87d40b77b4e4beb7e3d0a9ea396ad918a81e8


[ROCm/hip commit: 5476c9877b]
2021-04-14 12:38:46 -04:00
Rupam Chetia c1f57da073 SWDEV-238517 - [dtest] Adding additional scenarios for block and grid dimension.
1. Corner case and negative test scenarios added for block and grid dimension.

Change-Id: I094faf02570fec101f688462712934b94ceb37e1


[ROCm/hip commit: b1d78e4096]
2021-04-07 01:44:39 -04:00
Rupam Chetia 03a8b74aa9 SWDEV-238517 - [dtest] Test for Multiple Target Architecture Code Object
Added a test to generate a code object for multiple target
architectures (including for the current device),
load and execute the kernel.

SWDEV-238517 for enhancing hip unit tests

Change-Id: I509d01124abdc0495cfc770ab5508738f108c91c


[ROCm/hip commit: 7c20d3e4e4]
2021-02-15 06:41:24 -05: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 285775c1b5 SWDEV-271406 - Remove unecessary hip_ext.h
tests/src/runtimeApi/module/hipModuleLaunchKernel.cpp doesn't
need hip_ext.h which will fail cuda building. So remove it

Change-Id: Icf5763449ccec839d9efda90ffe3a86fb53bdb85


[ROCm/hip commit: 9996ebb641]
2021-02-08 14:33:04 -05:00
agodavar 637cefb59f SWDEV-268552 - HIP sample segfaults during hipModuleLoad, fix mmap bug
Change-Id: I51c6061e7ac6b2524586d96fdd69b9f084b1906a


[ROCm/hip commit: aac12d1bd9]
2021-01-27 23:39:50 -05:00
DURGESH KROTTAPALLI 76eb4b7b1e [dtest] Kernel Execution time fix for hipExtLaunchKernelGGL and hipExtModuleLaunchKernel API's
Fix for kernel execution time using clock rate

SWDEV-238517 for enhancing hip unit tests

Change-Id: Id06df31387ecab96f219e0c1fbcdda1609f75605


[ROCm/hip commit: 0b871a24f6]
2021-01-15 01:58:22 -05:00
DURGESH KROTTAPALLI 2d6af3d103 [dtest] Tests for hipExtLaunchKernelGGL APIs
Added test scenarios for hipExtLaunchKernelGGL
1. verify kernel execution time using events
   passed through argument
2. Verify the API by disabling time flag in
   event creation.

SWDEV-238517 for enhancing hip unit tests

Change-Id: I755adc34a25c58b68041fc927bbffd2a9e6eafde


[ROCm/hip commit: d1c921ffca]
2021-01-08 00:16:54 -05:00
DURGESH KROTTAPALLI d017c25361 [dtest] Tests for hipExtModuleLaunchKernel APIs
Added test scenarios for hipExtModuleLaunchKernel/hipModuleLaunchKernel APIs

 1. Negative Test Scenarios for hipExtModuleLaunchKernel API
 2. Negative Test Scenarios for hipModuleLaunchKernel API
 3. hipExtModuleLaunchKernel API Concurrency Verification
    using global variable
 4. hipExtModuleLaunchKernel API Concurrency Verification
    using total time taken by kernels.
 5. hipExtModuleLaunchKernel API verifying the kernel execution time
    of a particular kernel
 6. hipExtModuleLaunchKernel API verifying by disabling the
    time flag during event creation

SWDEV-238517 for enhancing hip unit tests

Change-Id: I33bbab152d47beba62065c461a07cbcacdc01d97


[ROCm/hip commit: ba3fff4fcd]
2021-01-08 00:05:57 -05:00
Rupam Chetia facdc585cb [dtest] Enabling all negative tests for hipModule* APIs
Enabling all negative test cases for amd as they are functional now
SWDEV-238517 for enhancing hip unit tests

Change-Id: I0bdbf8c192ef94588403c8f027c0399dd5480a00


[ROCm/hip commit: a6d7c7c8ff]
2021-01-07 23:50:56 -05:00
Rupam Chetia d9a448a070 [dtest] Tests added for V3 and V4 Code Objects with Static Lds
- Added test for V3 Static Lds code object with sramecc/xnack settings.
- Added test for V4 Static Lds code object.

SWDEV-238517 for enhancing hip unit tests

Change-Id: Ibc4f7e12033dec231d6834ccdd983e3b9e001d60


[ROCm/hip commit: 4c2e91c772]
2021-01-07 23:19:02 -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
Rupam Chetia 3e2dc0d39f [dtest] Tests for hipModuleGetTexRef() API
1. Negative Test Cases
2. API functionality test using multiple streams.
3. API functionality validation using multiple GPUs.
4. Setting hipTexRefSetFlags() with HIP_TRSF_READ_AS_INTEGER flag instead of 0 as suggested in SWDEV-256096.
5. Enabling test cases 0x03 (short) and 0x04 (char).
6. Implemented external code review comments.

SWDEV-238517 for enhancing hip unit tests

Change-Id: If42796047ec1cf2e3695dc2b7f40a2d9dd50f5bd


[ROCm/hip commit: 9d92c90b55]
2020-11-26 06:51:49 -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
Lakhan singh Thakur 66aba3ea21 [dtest] Adding Test case for hipFuncSetSharedMemConfig() and hipFuncSetAttribute()
SWDEV-251504 - QA task for validation

Change-Id: I11ed98f648352cb32161c41290516c77231236bc


[ROCm/hip commit: 548ec20ffd]
2020-10-13 11:11:00 -04:00
Rupam Chetia 3e98b823d3 [dtest] hipModuleLoad and related API tests
APIs: hipModuleLoad, hipModuleLoadData and hipModuleLoadDataEx,
      hipModuleGetGlobal(), hipModuleGetFunction
Functional and negative tests
Repeated call to ModuleLoadXX/ModuleUnloadXX
Few tests are disabled now, will be enabled when functional

SWDEV-238517 for enhancing hip unit tests

Change-Id: I65c12027e32db80213468fdee1c5cc1aa3e60bfd


[ROCm/hip commit: 71ba35eb2c]
2020-10-13 11:10:11 -04:00
Jason Tang 69b0429a5e Add hipStreamSynchronize to hipModuleLoadDataMultThreadOnMultGPU test
hipStreamDestroy() by definition doesn't guarantee waiting for all stream operations.

Change-Id: Ibfd21c48d71741ebcbcb9898c8b5ac235bdc570b


[ROCm/hip commit: 2299459ce0]
2020-10-08 11:06:39 -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
Aryan Salmanpour 40d44e2c8d [dtest] move all the cooperative related tests into one location
Change-Id: I9b44027d795ebfbf42f78af8e69d26ac8109692a


[ROCm/hip commit: e1cb711e66]
2020-10-01 16:01:46 -04:00
Todd tiantuo Li 33249339d1 SWDEV-240803 - add test for hipFuncSetSharedMemConfig
Change-Id: I150b65a548ee9bf8d7e079b3db2e73958747c3a0


[ROCm/hip commit: 66efc13d5c]
2020-09-21 17:26:51 -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
Jatin Chaudhary 2982f07b9c Fixing/Disabling tests on nvcc path
Change-Id: I7ed4a1246943867482ff595d5f98bb25bd79074b


[ROCm/hip commit: e7eaafe165]
2020-07-30 00:39:07 -04:00
kjayapra-amd f2c6f3bf63 SWDEV-236178 - Remove __hip_pinned_shadow reference from dtests and add hipModuleUnload for all corresponding hipModuleLoad calls.
Change-Id: I405789b430ffbb8fccda1cebdb5d18e83a85c926


[ROCm/hip commit: 0dd6123998]
2020-06-11 22:34:36 -04:00
kjayapra-amd 37508980de SWDEV-236178 - Reorganizing Platform/Modules code for easy access.
Change-Id: Ie8920260ffc4ff01e44b48af8cec9ea5aed1aa9b


[ROCm/hip commit: 20f05c4228]
2020-06-11 10:11:20 -04:00
rohit pathania 791e62287c [ dtest ] hipModuleLaunchKernel multiThreaded n multiGPU scenarios
1.Added hipModuleLaunchKernel multithreaded multi GPU scenario.
2.removed hipCtxCreate API from earlier test as it is deprecated.

SWDEV-238517 for enhancing hip unit tests

Change-Id: Id102d80887b6ff61a59938dbeb9fa2a26a3275b2


[ROCm/hip commit: cc6a87e9e3]
2020-06-05 09:40:58 -04:00
German Andryeyev 80bd9632ad Correct mgpu coop launch test
When the original size is devided accross all GPUs rounding can
occur, causing incorrect validation. Readjust the final value
for comparison to the new size accordingly.

Change-Id: I9b42149e33dfcb328de7419e546a0202a69a8610


[ROCm/hip commit: 20f0e36041]
2020-05-13 14:39:11 -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 8e137a6ec1 Merge in the rocclr based hip runtime (#2032)
* Merge master-next changes in master (include vdi development in master branch)



[ROCm/hip commit: a0b5dfd625]
2020-04-23 09:12:06 -07:00