提交图

805 次代码提交

作者 SHA1 备注 提交日期
Rahul Garg 3b5dac1d9d Add HIP init in hipFuncGetAttributes (#1262)
* Add HIP init in hipFuncGetAttributes

* [dtest]Remove explicit hip init call in hipFuncGetAttributes dtest


[ROCm/clr commit: c610159b85]
2019-07-31 15:42:08 +00:00
ansurya 733178f492 Testcase to validate signed/unsigned char,short as normalized float (#1267)
* Testcase to validate signed/unsigned char,short as normalized float

* corrected test_common.cpp file path


[ROCm/clr commit: 440c5f1677]
2019-07-31 05:02:35 +00:00
Aryan Salmanpour 8b0c37a9ce [hip][tests] add a unit test for using hipExtLaunchMultiKernelMultiDevice API (#1250)
[ROCm/clr commit: 571af6d85b]
2019-07-24 07:57:39 +00:00
Aaron Enye Shi 73af1ac4bd Add GFX908 specific changes to HIP (#1229)
* Add GFX908 specific for HIP

* Fix missing __halfTest in hipTestNativeHalf


[ROCm/clr commit: 8c82f9db77]
2019-07-24 07:51:17 +00:00
Maneesh Gupta a1e4200ee8 [dtests] Fix complex_loading_behavior.cpp build issues on nvcc path (#1242)
[ROCm/clr commit: 7feda764b6]
2019-07-24 07:49:39 +00:00
Aaron Enye Shi 99ca4c2483 Fix hipMemcpy-size test running out of Host Mem (#1224)
* Fix hipMemcpy-size test running out of Host Mem

The hipMemcpy-size uses a maxElem calculated from the total GPU mem /8. Then it will allocate 4 times that amount of host memory. This tests begins failing when there is not enough host memory, such as on systems with 32GB GPU mem, and 16GB RAM. This fixes the test if not enough host memory is available on the system.

* Add windows support to hipMemcpy-size fix

* avoid linking extra libs for windows

* HIPMemcpy-size Remove freeCPU including swap


[ROCm/clr commit: c56876cc19]
2019-07-24 07:49:20 +00:00
Maneesh Gupta f0f831daa7 [hit] Workaround for %cc and %cxx mappings. (#1233)
* [hit] Workaround for %cc and %cxx mappings.

HIP CMakeLists.txt modifies CMAKE_C_COMPILER and CMAKE_CXX_COMPILER.
This messes up any dtests that want to test against cc/c++.

So hardcode %cc to /usr/bin/cc and %cxx to /usr/bin/c++ for now till
we come up with a better solution.

Change-Id: I7dce93ce8360191e612a94e3a735e5612ac27ab5

* [hit] Add auto-variable %hip-path to syntax for BUILD_CMD

Change-Id: Id097a183fbce2b2c9691d0180d3304dd17a4e016


[ROCm/clr commit: af9aae6b4e]
2019-07-19 04:45:56 +00:00
ansurya af2df395a0 [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


[ROCm/clr commit: f566bec546]
2019-07-19 04:45:20 +00:00
ansurya 8b8946f78b Add Max Texture 1D,2D,3D device properties (#1226)
* Add Max Texture 1D,2D,3D device properties

* Corrected testcase to use enums defined in hipDeviceAttribute_t

* Added texture 1D,2D and 3D support for NVIDIA path


[ROCm/clr commit: 00aa42e05f]
2019-07-18 03:18:50 +00:00
Maneesh Gupta 61833b948d [dtests] Fix typo in hipAPIStreamDisable.cpp (#1227)
Change-Id: Ib88a6be49ba192578129bb88ad09817839981398

[ROCm/clr commit: d206d66dfe]
2019-07-17 07:28:38 +00:00
Maneesh Gupta ccf76633f9 [dtests] Temporarily disable failing tests (#1218)
Change-Id: I7bb36a964c635bfbdf67484f3454d8fff7168eb2

[ROCm/clr commit: 4d2f2396aa]
2019-07-17 07:28:21 +00:00
Evgeny Mankov 096aad2de2 Merge pull request #1220 from emankov/master
[HIP][HIPIFY] Split HIP_ARRAY_DESCRIPTOR struct to HIP_ARRAY_DESCRIPTOR and HIP_ARRAY3D_DESCRIPTOR

[ROCm/clr commit: c978af3b13]
2019-07-16 18:15:44 +03:00
kpyzhov 71297fa621 Added gfx906 kernel binary to the HIPFB file for hipModule test. (#1215)
[ROCm/clr commit: 728ce926d9]
2019-07-12 03:13:45 +00:00
Evgeny Mankov b5f0cdaa7b [HIP][HIPIFY] Split HIP_ARRAY_DESCRIPTOR struct to HIP_ARRAY_DESCRIPTOR and HIP_ARRAY3D_DESCRIPTOR
[Reason] To be compatible with CUDA [#1133]

Update HIP code, hipify-clang, tests and docs

[TODO] Add support of the corresponding functions on nvcc fallback path


[ROCm/clr commit: f0832fd968]
2019-07-11 14:58:16 +03:00
Yaxun (Sam) Liu 2c8502f1db Add __hip_pinned_shadow__ for hip-clang and fix texture reference tests (#1200)
[ROCm/clr commit: 3169f3a881]
2019-07-03 08:51:59 +00:00
Alex Voicu 1e12e00009 Put 3-wide vector types on a ketogenic diet. (#1180)
* Put 3-wide vector types on a ketogenic diet.

* Remove needless include.

* Do not be narrow-minded.

* Do not be narrow-minded.

* Put the C people on a diet too.


[ROCm/clr commit: 87eac86298]
2019-06-25 06:32:09 +05:30
wkwchau 81b5ea1c4a 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


[ROCm/clr commit: 28c34ead70]
2019-06-20 05:58:29 +05:30
Maneesh Gupta 33b6b0bba7 [dtests] Temporarily disable hiprtc tests
Change-Id: I87c0c01837e7b59b11d99fb94d679a765f914da5


[ROCm/clr commit: 165d73de9a]
2019-05-31 16:39:33 +05:30
Maneesh Gupta f9a832ce3f Merge pull request #1124 from kpyzhov/hipModule-test
Updated kernel binary file for hipModule test.

[ROCm/clr commit: f30446c4bc]
2019-05-24 14:16:03 +05:30
Maneesh Gupta af0765080c Merge pull request #1121 from kpyzhov/hipStreamSync2-test
Disable hipStreamSync2 test for hip-clang.

[ROCm/clr commit: c289973030]
2019-05-24 14:15:54 +05:30
Evgeny Mankov fa2ec209ab [HIPIFY] Add device texture fetch functions support
+ Add a corresponding reverse engineered sample tex2dKernel with texture template


[ROCm/clr commit: 7db992cf44]
2019-05-23 12:47:08 +03:00
Konstantin Pyzhov bd9f78fe4e Updated kernel binary file for hipModule test.
[ROCm/clr commit: d2125f0325]
2019-05-21 13:21:48 -04:00
Evgeny Mankov 3e0fa665f7 [HIPIFY][tests] Add reverse engineered HIP sample "peer2peer"
+ Fix typo in sample "stream"


[ROCm/clr commit: 5c205b75f5]
2019-05-20 17:16:11 +03:00
Konstantin Pyzhov 05746f20e9 Disable hipStreamSync2 test for hip-clang.
[ROCm/clr commit: adf3b8774e]
2019-05-20 02:13:30 -04:00
Evgeny Mankov 9d0ac6be5e Merge pull request #1115 from emankov/master
[HIPIFY][cuDNN] Add cudnnGetFilter4dDescriptor support

[ROCm/clr commit: 21518887bc]
2019-05-16 16:39:34 +03:00
Evgeny Mankov 76c52aa429 [HIPIFY][cuDNN] Add cudnnGetFilter4dDescriptor support
+ Update cudnn_convolution_forward test accordingly


[ROCm/clr commit: 02f8dfe7d8]
2019-05-16 16:36:23 +03:00
Alex Voicu a4a3132c64 Add HIPRTC, glorious ersatz for NVRTC (#1097)
* Add ersatz for NVRTC.

* Fix extraneous paren and use correct namespace.

* Use lowerCamelCase (yuck, yuck) consistently.

* Link against FS when building hiprtc lib.

* Correctly mark Manipulators. Fix dual compile.

* Add unit tests. Extend HIT to accept linker options.

* Make sure the HIPRTC library is installed.

* Better logging. Try to auto-detect the target.

* Stop specifying the target explicitly.

* Add missing flavour of `hipModuleLaunchKernel`.

* Program was already destroyed.

* Don't use `--genco`. Fix mangled name trimming.

* Fix HIPRTC breakage due to upstream noise.

* [dtests] Replace RUN -> TEST in hiprtc tests

Change-Id: Ie499e92dfe4e5c94634b1c2b76cf52d241bcfea3

* [hit] Set HIP_PATH to HIP_ROOT_DIR for all tests

Change-Id: Ib0ad1f99bc71c03e363e055dd508a7a4a210680a


[ROCm/clr commit: a538eb705a]
2019-05-16 18:28:54 +05:30
Evgeny Mankov 355f49a850 [HIPIFY][tests] Add reverse engineered HIP sample "stream"
+ Add additional checks for extern __shared__ due to [#1109]


[ROCm/clr commit: 7cc12df514]
2019-05-15 20:17:03 +03:00
Evgeny Mankov bbe9275e38 [HIPIFY][fix][#1109] Do not preserve extern __shared__ for IncompleteArrayType
+ Update tests accordingly


[ROCm/clr commit: bf65120156]
2019-05-15 20:05:56 +03:00
Konstantin Pyzhov 5bb9455f51 Upload pre-built kernel binary for hipModule test.
[ROCm/clr commit: 6242377a5c]
2019-05-15 07:19:40 -04:00
Evgeny Mankov 7a5a838e80 [HIPIFY][tests] Add reverse engineered HIP sample Profiler
+ Add missing cuda_profiler_api.h to hip/hip_profile.h transformation.
NOTE: HIP Profiler API is under development. This is NOT WORKING example.
TODO: Find out a way to generate HIP_SCOPED_MARKER, HIP_BEGIN_MARKER, HIP_END_MARKER, declared in hip/hip_profile.h in particular place (signatures are to obtain).


[ROCm/clr commit: 5e49c25faa]
2019-05-14 16:43:44 +03:00
Evgeny Mankov 8c12edcf65 [HIPIFY][tests] Add reverse engineered HIP sample hipEvent
[ROCm/clr commit: 9860dac7fa]
2019-05-13 22:12:43 +03:00
emankov 39b28d7623 [HIPIFY][tests] Add reverse engineered HIP sample MatrixTranspose
[ROCm/clr commit: cdc76af186]
2019-05-13 19:37:18 +03:00
Maneesh Gupta 3d098c6a1c [dtests] Fix hipModule test for nvcc path
Change-Id: If918b87b848a825242e06b0d552a7be188a1c4b6


[ROCm/clr commit: 6e573ba430]
2019-05-09 18:17:19 +05:30
Maneesh Gupta 3b75006961 [dtests] Add complex_loading_behavior test
Change-Id: Iadf135cb727a1a3761abef20336d652b159c7dcd


[ROCm/clr commit: e95f7fc1f8]
2019-05-09 18:03:42 +05:30
Maneesh Gupta f46fafd3a4 [dtests] Add hipModule test to unit tests
Change-Id: I1dac38f8580265e2e9c82d88e4f070a2ff87f60b


[ROCm/clr commit: 4b38188e1e]
2019-05-09 11:36:46 +05:30
Maneesh Gupta 1b896685a3 [hit] Add support for BUILD_CMD
[ROCm/clr commit: dac20b7736]
2019-05-09 11:36:26 +05:30
Maneesh Gupta 68cf672441 [hit] Remove CUSTOM_CMD
Change-Id: Ia156fe6aab9cfcc11284823ea5131e33eaf962bc


[ROCm/clr commit: db52b0f60f]
2019-05-09 09:59:18 +05:30
Maneesh Gupta 74110bbd43 [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074


[ROCm/clr commit: 53dd1df3fa]
2019-05-09 09:59:18 +05:30
Maneesh Gupta 532725c9c8 Merge pull request #1075 from mhbliao/hliao/master/test_fix2
[test] Add device variant of `std::declval`.

[ROCm/clr commit: 51e158c633]
2019-05-07 16:15:01 +05:30
Maneesh Gupta dce65678d7 Merge pull request #1074 from mhbliao/hliao/master/test_fix
[test] Use explicit cast for address space cast.

[ROCm/clr commit: 7f759750d1]
2019-05-07 16:09:15 +05:30
Maneesh Gupta fb08e0f25e Merge pull request #1073 from kpyzhov/multi-thread-device-test
hipMultiThreadDevice test: Reduced maximum number of created HIP stre…

[ROCm/clr commit: d71afeccc8]
2019-05-07 16:08:37 +05:30
Maneesh Gupta e514de5b33 Merge pull request #1072 from kpyzhov/master
Refined hipSetDevice test.

[ROCm/clr commit: 8f352427f4]
2019-05-07 16:07:36 +05:30
Maneesh Gupta 4a4745e466 Merge pull request #1069 from mhbliao/hliao/master/test_cleanup
[test] Remove unused common routines.

[ROCm/clr commit: 0fffbbe67a]
2019-05-07 16:02:57 +05:30
Michael LIAO f644d4daaa [test] Add device variant of std::declval.
- Current clang disallows any invocation of wrong-side functions even
  under context with type-inspection only. Work around that by adding a
  variant of `std::decl` with `__device__` attribute.


[ROCm/clr commit: 32f69c8bc4]
2019-05-03 15:58:31 -04:00
Michael LIAO fa74e75fc1 [test] Use explicit cast for address space cast.
[ROCm/clr commit: a27877794f]
2019-05-03 14:56:00 -04:00
Maneesh Gupta c73c864fdf Merge pull request #1058 from mhbliao/hliao/master/devfunc
[Device Function] Fix implementation

[ROCm/clr commit: ad070d4da5]
2019-05-03 17:47:51 +05:30
Konstantin Pyzhov 1be1dd207a hipMultiThreadDevice test: Reduced maximum number of created HIP streams on Windows.
[ROCm/clr commit: e04e408a37]
2019-05-03 05:43:30 -04:00
Konstantin Pyzhov b2e3880696 Refined hipSetDevice test.
[ROCm/clr commit: 29fd3812e5]
2019-05-03 05:39:45 -04:00
Michael LIAO 9823184397 [test] Remove unused common routines.
- Remove used common routines, which variadic functions, not supported
  feature, are used.


[ROCm/clr commit: aad19f6171]
2019-05-02 12:34:07 -04:00