AI/rocm-systems
2
0
انشعاب 0
کد مسائل تقاضاهای واکشی Actions Packages پروژه‌ها انتشارها دانشنامه فعالیت
4,931 کامیت‌ها 3 شاخه‎ها 0 برچسب‎ها
33da3f5c5061128c9ef887c66606d653ddaa3723
نمودار کامیت

47 کامیت‌ها

مولف SHA1 پیام تاریخ
Payam 3d64a38953 reverting part of http://gerrit-git.amd.com/c/compute/ec/hip/+/326145 
the test still fails

Change-Id: I2e5968115a717e8482be670d9fb8472e391922d7
 2020-03-04 13:49:58 -05:00
agodavar 3479847d16 Enable tests hipTestDeviceSymbol,hipTestConstant and p2p_copy_coherency on hip-vdi 
SWDEV-225266: [HIP-VDI] HIP-VDI disabled tests (p2p_copy_coherency.cpp)
SWDEV-225388: hipTestDeviceSymbol.cpp & hipTestConstant.cpp failed to build on hip-vdi

For hipTestDeviceSymbol.cpp & hipTestConstant.cpp tests:
Currently "__HIP_VDI__" flag is enabled in CMakeLists.txt, but when application is compiled with hipcc,  
__HIP_VDI__ is not defined to differentiate if compiled for VDI/HCC for headers.

For ./src/runtimeApi/memory/p2p_copy_coherency.cpp:
Fixed compilation issue to include only when compile for HCC runtime "<hc_am.hpp> not found"
Currently test is disabled to run on all platforms. When validated on multi-GPU machine,
memcpy between multiple GPUs via GPU synchronization is not working on hcc and vdi path.
Need to validate on nvidia machine to know if test is valid. Disabled GPU synchronization test for now.

For ./src/runtimeApi/module/hipModuleTexture2dDrv.cpp:
updated test to generate tex2d_kernel.code object in build directory. Currently ctest looks for it in build directory.

Change-Id: I629d395a919c2440d921422716944c7940ed6010
 2020-03-04 10:07:09 -05:00
Vladislav Sytchenko b910a7ff26 SWDEV-219799 
Add missing __hip_pinned_shadow__ attribute to the hipModuleTexture2dDrv test.

Change-Id: I2c213a4108611c1af691388f268cac429b81a313
 2020-03-03 11:49:00 -05:00
Payam f4401ff2b5 removing 3 tests temporarily to enable hiptests 
Change-Id: I8c45791aaf88628850462aff90979c147cb85f64
 2020-02-25 19:01:34 -05:00
Tao Sang ed56e605d4 Add __hip_pinned_shadow__ for texture 
Add missing __hip_pinned_shadow__ for texture in tex2d_kernel test.

Change-Id: Iefc96084fec8f84a1d1bb979998ffb95b4011f0b
 2020-02-20 20:01:28 -05:00
Tao Sang b3f445c0f5 Temporarily comment out Hcc-specific APIs for CLang compiler 
Temporarily comment out Hcc-specific template functions
hipExtLaunchKernelGGL and hipOccupancyMaxPotentialBlockSize for CLang
compiler so that all test cases under hip/samples can be built
successfully for Clang + Hip/Hcc runtime.

Change-Id: Iafc761257be4a7b34eafa6759a01f369570cd6ce
 2020-02-16 22:26:47 -05:00
Payam fabe62e31f removing oocupancy tests from hip-vdi for now 
Change-Id: I06e966d07021af87fa2c195e4bbaf6bcc336658d
 2020-02-13 21:40:06 -05:00
Laurent Morichetti 2cf3257795 Merge branch 'master' into amd-master-next 
Change-Id: Ibb7775e7acd263d2ece40a241517bbd15976fdd4
 2020-02-12 00:14:07 -08:00
Maneesh Gupta f8e1c01900 Revert "Match Occupancy APIs syntax with CUDA (#1625)" (#1857) 
Reverting this for now till we figure out how to avoid the build
breakage.

This reverts commit fa98798b63.
 2020-02-10 10:45:28 +05:30
Payam e4e8c4b74b Excluding vdi platform for now from the following tests so we can build 
Change-Id: I651255c2515a62c8bdfdd17a3ac85c3d66a5761b
 2020-02-07 02:16:05 -05:00
lthakur 4d472b777f [dtest] Update hipLaunchCoopMultiKernel.cpp (#1844) 
used reinterpret_cast<uint32_t*> for numBlocks, as expected by hipOccupancyMaxActiveBlocksPerMultiprocessor() api.
 2020-02-04 19:37:38 +05:30
gandryey 48d1f766d5 [dtest] RCCL multi device launch test (#1731) 
Simple test for hipLaunchCooperativeKernelMultiDevice API.
 2020-02-04 08:53:43 +05:30
satyanveshd fa98798b63 Match Occupancy APIs syntax with CUDA (#1625) 
* Match Occupancy APIs syntax with CUDA and fix tests using these APIs
 2020-01-29 13:05:53 -08:00
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
Rahul Garg 188752b2cb [dtest] Rename hipExtLaunchMultiKernelMultiDevice dtest (#1671) 2019-11-19 09:41:13 -08:00
Alex Voicu 69e74c3e96 Add support for extended launch syntax. (#1530) 
* Add support for extended launch syntax.

* Add unit test.

* Fix typo

* hipExtLaunchKernelGGL lives in hip_ext.h

Change-Id: Ice32dab0d43475fda65c6a910c11416871a8f2ff

* [dtest] remove redundant include from hipModuleGetGlobal dtest
 2019-11-16 22:24:07 -08:00
Rahul Garg 579a4f36fa Rename hip/hip_hcc.h to hip/hip_ext.h (#1341) 
* Rename hip/hip_hcc.h to hip/hip_ext.h

* Deprecate hip_hcc.h
 2019-11-07 13:17:10 +05:30
Aryan Salmanpour cf92fae9e6 [hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel (#1613) 2019-11-05 12:32:46 +05:30
Rahul Garg 55f2a38120 Formatting changes 2019-10-30 18:12:51 -07:00
Rahul Garg 4ab71216b4 Formatting changes ,variable name and check update 2019-10-30 18:09:21 -07:00
amd-lthakur 4239c94fe5 Excluded the test case for nvcc platform 2019-10-25 15:52:11 +05:30
amd-lthakur 564418c308 Refactored the file as suggested 2019-10-25 10:44:38 +05:30
amd-lthakur 318df5c36b Update matmul.cpp 2019-10-25 09:22:07 +05:30
amd-lthakur cd25149225 Update hipExtModuleLaunchKernel.cpp 2019-10-25 09:19:49 +05:30
amd-lthakur 8b496e4715 Adding a directed test case for hipExtModuleLaunchKernel() api. 2019-10-24 15:06:28 +05:30
ansurya 87834500b9 Fix for directed tests failure (#1511) 
directed_tests/runtimeApi/module/hipLaunchCooperativeKernel.tst - Disabling test temporarily until driver support is available.
directed_tests/runtimeApi/memory/hipArray.tst - Disabling test temporarily to reimplement it correctly.
 2019-10-10 19:58:41 +05:30
AlexBinXie b3e6ba50c3 [hip] Added gfx803,gfx1010,gfx1012 kernel binary hipModule test. (#1444) 
This is to address hipModule test seg fault in GFX1010
 2019-09-30 10:38:37 +05:30
Aryan Salmanpour 48880a017e [hip][tests] add a unit test for testing hipLaunchCooperativeKernel (#1361) 
* [hip][tests] add a unit test for testing hipLaunchCooperativeKernel

* use __ockl_grid_sync function

* remove already defined __ockl_grid_sync function

* use sync function for grid synchronization
 2019-09-16 08:31:09 +00:00
wkwchau 4b18b321f7 Added support of hipOccupancyMaxActiveBlocksPerMultiprocessor & hipOc… (#1240) 
* Added support of hipOccupancyMaxActiveBlocksPerMultiprocessor & hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags APIs

* Taking into account of SGPR usage to determine the max active blocks in hipOccupancyMaxActiveBlocksPerMultiprocessor()
 2019-08-01 08:58:48 +00:00
Rahul Garg 0517c30507 Add HIP init in hipFuncGetAttributes (#1262) 
* Add HIP init in hipFuncGetAttributes

* [dtest]Remove explicit hip init call in hipFuncGetAttributes dtest
 2019-07-31 15:42:08 +00:00
Aryan Salmanpour f3c4952f80 [hip][tests] add a unit test for using hipExtLaunchMultiKernelMultiDevice API (#1250) 2019-07-24 07:57:39 +00:00
ansurya fa4d6b353a [HIP][Tests] Added new testcases for Module API (#1150) 
* [HIP][tests] New testcases for module api

* [HIP][Tests]Support for CUDA devices

* Updated tests as per latest master & test GetGlobal to work on all platforms
 2019-07-19 04:45:20 +00:00
kpyzhov e6a8d1daee Added gfx906 kernel binary to the HIPFB file for hipModule test. (#1215) 2019-07-12 03:13:45 +00:00
wkwchau d492f1fd6b Implement the hipOccupancyMaxPotentialBlockSize function (#1162) 
* Implement the hipOccupancyMaxPotentialBlockSize function

* Replaced hipGetDeviceProperties() call by ihipGetDeviceProperties() in ihipOccupancyMaxPotentialBlockSize()

* Add test for hipOccupancyMaxPotentialBlockSize in Module API

* Added extern declaration for ihipGetDeviceProperties() to be accessed inside ihipOccupancyMaxPotentialBlockSize()

* fixed hipOccupancyMaxPotentialBlockSize test build issue

* Fix hipOccupancyMaxPotentialBlockSize dtest

* Add BUILD_CMD in hipOccupancyMaxPotentialBlockSize dtest

* Revert "Add BUILD_CMD in hipOccupancyMaxPotentialBlockSize dtest"

This reverts commit 0480ff56f1441fc515d2c26ce33783e303423938.

* Disable hipOccupancyMaxPotentialBlockSize dtest on NVCC

* move extern declaration of ihipGetDeviceProperties to hip_module.cpp

* Update the limiation of 32 wavefronts per CU and 800/512 SGPRs for VI/pre-VI chips to calculate the occupancy
 2019-06-20 05:58:29 +05:30
Konstantin Pyzhov a8b07ada2f Updated kernel binary file for hipModule test. 2019-05-21 13:21:48 -04:00
Konstantin Pyzhov c8f92bebf3 Upload pre-built kernel binary for hipModule test. 2019-05-15 07:19:40 -04:00
Maneesh Gupta 88abfde2f8 [dtests] Fix hipModule test for nvcc path 
Change-Id: If918b87b848a825242e06b0d552a7be188a1c4b6
 2019-05-09 18:17:19 +05:30
Maneesh Gupta 79843f3b12 [dtests] Add hipModule test to unit tests 
Change-Id: I1dac38f8580265e2e9c82d88e4f070a2ff87f60b
 2019-05-09 11:36:46 +05:30
Maneesh Gupta 9f2d1453fb [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED 
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074
 2019-05-09 09:59:18 +05:30
Maneesh Gupta 8b93cd67a6 [dtests] Fix nvcc path build errors in hipFuncGetAttributes.tst 
Change-Id: I000bed69162897f7b6edd733ed6e9acc93beb0ed
 2018-05-30 11:26:11 +05:30
Alex Voicu 13274ce559 Add support for the hipFuncGetAttributes interface. 2018-05-11 03:35:10 +01:00
Maneesh Gupta 1ba06f63c4 Apply .clangformat to all repo source files 
Change-Id: I7e79c6058f0303f9a98911e3b7dd2e8596079344
 2018-03-12 11:29:03 +05:30
Alex Voicu cffd0e14eb 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. 2017-11-19 01:54:12 +00:00
Aditya Atluri fc6248ce82 added hipFuncSetCacheConfig API for nvcc path 
Change-Id: I87fae35bc0e10a0dca5ae1c5015fe5d9e52a1d0d
 2017-04-26 18:56:57 -05:00
Aditya Atluri 378eb3fa55 v2: Fixed hipModule memory management 
1. Changed test to assert for same hipFunction values
2. Added better memory management for hipModule

Change-Id: I10d7aef13c215a2211e262f3c79017f26a17d9a7
 2017-02-10 13:32:13 -06:00
Aditya Atluri 6fd3daed30 fixed hipFunction memory management 
Change-Id: I7ebb323419bcd220ebd6466a8eb38e7bfdb1520a
 2017-02-09 17:22:55 -06: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