コミットグラフ

1106 コミット

作成者 SHA1 メッセージ 日付
Alex Voicu 1baaf44179 __half2 should walk like CUDA and talk like CUDA
[ROCm/hip commit: e5bd00d06b]
2019-11-06 02:43:04 +02:00
Michael LIAO e250f76183 Use portable macro for deprecation message.
[ROCm/hip commit: a7f311cc14]
2019-11-05 11:51:00 -05:00
Rahul Garg 1b8973d6be Deprecate HIP Markers (#1622)
* Deprecate HIP markers

* Deprecate profiler start/stop


[ROCm/hip commit: 54fab7c35c]
2019-11-05 12:32:59 +05:30
Alex Voicu e87f9b1944 Separate volatile for clarity. Handle assignment.
[ROCm/hip commit: 99b9d5449f]
2019-11-02 22:02:08 +02:00
Alex Voicu b30a42f678 Accessors should work even when oddly volatile.
[ROCm/hip commit: ee5097f2c2]
2019-11-01 22:18:01 +02:00
Rahul Garg 7e742b1216 Merge pull request #1515 from ansurya/tex_unbind_issue_fix
Fix undefined ref to hipUnbindTexture for texture types

[ROCm/hip commit: ba8105e0cd]
2019-10-30 17:54:15 -07:00
Michael LIAO 2bff0748cd [HIP] Correct headers and add missing function templates for hip-clang.
- Fix 2 runtime API prototypes
  `hipOccupancyMaxActiveBlocksPerMultiprocessor` and
  `hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags`
- Add missing function templates of them in hip-clang.


[ROCm/hip commit: 5c8a7521f4]
2019-10-29 22:00:11 -04:00
Rahul Garg 70449cfa92 Revert "Fix occupany APIs (#1560)"
This reverts commit 4f23f9cb18.


[ROCm/hip commit: e4a1e44162]
2019-10-29 11:41:08 -07:00
Anusha Godavarthy Surya 5c77b7d19a Merge branch 'master' into tex_unbind_issue_fix
[ROCm/hip commit: 03623cc3f1]
2019-10-25 15:54:25 +05:30
Anusha Godavarthy Surya 196bdea9c0 merge from master
[ROCm/hip commit: 5f47e99ffe]
2019-10-25 15:52:09 +05:30
Alex Voicu 8460793117 Add missing operators, fix GCC compilation. (#1589)
[ROCm/hip commit: dabd939048]
2019-10-25 15:44:24 +05:30
Alex Voicu 2e9868d597 Fix deadlock, remove old __sync_* use. (#1584)
This fixes a deadlock introduced by the switch to TTAS loops, and is therefore mildly urgent (to prevent the CI from hoovering in the broken code).

[ROCm/hip commit: a855a13c22]
2019-10-25 15:44:17 +05:30
Rahul Garg c315da2028 Add hipMemcpy2DfromArray (#1510)
Adds hipMemcpy2DFromArray and hipMemcpy2DFromArrayAsync equivalent to cudaMemcpy2DFromArray and cudaMemcpy2DFromArrayAsync.

[ROCm/hip commit: 356765a223]
2019-10-25 15:43:33 +05:30
Anusha Godavarthy Surya 3007505d30 Merge branch 'master' into tex_unbind_issue_fix
[ROCm/hip commit: 259d8b4cdf]
2019-10-25 15:36:55 +05:30
Anusha Godavarthy Surya f51eeeb5de Fixed CI build failure
[ROCm/hip commit: ce04bdaa1a]
2019-10-25 12:21:41 +05:30
gandryey 4a7884105f Hip vdi profiling header (#1577)
Add HIP-VDI profiling interface for GPU timing collection.

[ROCm/hip commit: 81952ce5a7]
2019-10-24 17:45:42 +05:30
Alex Voicu 8f020907c7 Make CAS loops use the TTAS idiom. (#1573)
* Make CAS loops use the TTAS idiom.

* More efficient re-formulation of TTAS.

* Fix typo.

* The typo was not quite a typo


[ROCm/hip commit: 9ba25b42c8]
2019-10-24 17:45:20 +05:30
satyanveshd 4f23f9cb18 Fix occupany APIs (#1560)
Addresses SWDEV-205006 

[ROCm/hip commit: af351d7e1b]
2019-10-24 17:44:47 +05:30
searlmc1 4d668d5a52 Improve performance of v2 arg handling (#1539)
* Improve performance of v2 arg handling

* Missing change to `std::string`


[ROCm/hip commit: c4a51f3679]
2019-10-24 17:44:05 +05:30
Alex Voicu 52a5380263 Improve scalar access into vector types. (#1531)
The improvement is based on the ideas here: https://t0rakka.silvrback.com/simd-scalar-accessor. It yields significantly better ISA when the base's .xyzw members are used.

[ROCm/hip commit: 4a635add45]
2019-10-24 17:43:49 +05:30
Vladislav Sytchenko 370d039d24 Update the declarations of hipMemsetD8, hipMemsetD8Async, hipMemsetD16, hipMemsetD16Async. These functions are type aware and take in as their third argument the number of elements in the buffer, not the buffer size. Change the name of this argument from sizeBytes to count to align with the above description.
[ROCm/hip commit: 0b52c1d9d8]
2019-10-15 14:18:42 -04:00
Evgeny Mankov a4b08bcfa3 [HIP] Fix typo in a comment
[ROCm/hip commit: 28c23a7b1a]
2019-10-11 15:20:58 +03:00
Evgeny Mankov 0331004a44 [HIP][fix] Prefix libraryPropertyType to fix build of rocFFT and TensorFlow
[ROCm/hip commit: 337b7ce06a]
2019-10-11 15:18:08 +03:00
Evgeny Mankov 0ac55b1a9d [HIP] Introduce library_types.h as a common header for libs (#1509)
* [HIP] Introduce library_types.h as a common header for libs

[Reason]
Currently, hipFFT, hipBLAS and other HIP libs use their own data types, prefixed with HIPFFT or HIPBLAS, whereas in CUDA those types are common and declared in library_types.h

[TODO]
Switch hipFFT, hipBLAS and other HIP libs to use common library_types.h.

* [HIP] Move include for library_types.h to hip_runtime.h

[Reason]
Repeat CUDA's behaviour, where library_types.h is included in cuda_runtime.h


[ROCm/hip commit: 94eb4155dd]
2019-10-10 19:57:28 +05:30
Philip Salzmann aeba964a7e Fix uninitialized var in hipDeviceGetAttribute (#1497)
This fixes the usage of an uninitialized cdattr variable in hipDeviceGetAttribute for the CUDA backend when taking the switch default, as detailed in #1317.

Note that the directed_tests/runtimeApi/device/hipGetDeviceAttribute.tst test fails for me, but it already did before applying this patch. Let's see what CI says!

[ROCm/hip commit: 9ababa4276]
2019-10-04 13:39:19 +05:30
Rahul Garg 3b9b5fca8d Add texref get APIs support (#1471)
Added support for -
    hipTexRefGetArray
    hipTexRefGetAddressMode
    hipTexRefGetAddress



[ROCm/hip commit: bec725dec2]
2019-10-04 13:38:45 +05:30
Sarbojit2019 d8a79dda8c Removed definition of abs(), real() & imag() from hip_complex.h (#1448)
Addresses SWDEV-201461.

[ROCm/hip commit: 58a476abc2]
2019-10-04 13:38:02 +05:30
ansurya 66e94b1b1f Added new Memory API's (#1399)
Added new memory API's hipMemAllocPitch, hipMemAllocHost, hipMemsetD16, hipMemsetD16Async, hipMemsetD8Async
Modified to support all scenarios hipMemcpyParam2DAsync, hipMemcpyParam2D.


[ROCm/hip commit: ba9c6e13e4]
2019-10-04 13:36:31 +05:30
Yaxun (Sam) Liu 21201779c6 Fix cast of __half for HIP-clang (#1475)
[ROCm/hip commit: 56193a7828]
2019-09-30 10:40:42 +05:30
satyanveshd 25699d3b03 Map clock64() to __builtin_readcyclecounter() (#1473)
Fixes SWDEV-203215.

[ROCm/hip commit: 4b413739a9]
2019-09-30 10:40:31 +05:30
eshcherb a0dab5e09c to include hip_prof_str.h under USE_PROF_API macro (#1470)
[ROCm/hip commit: 8234da33b9]
2019-09-30 10:39:41 +05:30
Alex Voicu 4f1cb316c6 Optimise the gridDim.n * blockDim.m idiom (#1468)
[ROCm/hip commit: ab8fe8a3d8]
2019-09-30 10:39:23 +05:30
Yaxun (Sam) Liu 9ef2687f45 Add new kernel launching API for hip-clang
[ROCm/hip commit: 3c80389584]
2019-09-26 20:15:24 -04:00
Sarbojit2019 7f7a5a3712 [HIP] Add tccDriver info in hipDeviceProp
Fixes #1433.

[ROCm/hip commit: 0fa42af08c]
2019-09-26 13:53:33 +05:30
mhbliao 2a58af4380 [HIP] Remove a circular including. (#1418)
[ROCm/hip commit: 1f8c3bbd3b]
2019-09-16 08:32:47 +00:00
ansurya b5549f4397 Added new device attributes (#1377)
* Added new device attributes

* updated comment

* updated with new device attributes supported


[ROCm/hip commit: ceb734b917]
2019-09-16 08:31:30 +00:00
mhbliao 4913aec033 [hip] Stop using noduplicate and replace it with convergent. (#1390)
[ROCm/hip commit: 119ee4b671]
2019-09-05 10:03:43 +00:00
Yaxun (Sam) Liu 73b6fe599c Do not include cuda wappers for OMP for hip-clang (#1382)
[ROCm/hip commit: 8fe8fc18c0]
2019-09-03 05:13:59 +00:00
Sarbojit2019 fed6843ecf Removed hipLaunchKernel macro got missed in Merge (#1374)
[ROCm/hip commit: e1f9e08ea7]
2019-09-03 05:13:07 +00:00
Sarbojit2019 73e5c52d0d Updated hipErrorString and CUDAErrorTohipError (#1365)
[ROCm/hip commit: 0722704f35]
2019-08-29 01:02:59 +00:00
Sarbojit2019 74a3171c6b [HIP] Reclaiming hipLaunchKernel API (#1353)
* [HIP] Reclaiming hipLaunchKernel API

* Reclaiming hipLaunchKernel : Incorporated review comments

* Incorporated review comments

* Removed hipLaunchKernel Macro from nvcc path


[ROCm/hip commit: 5c4f78bac3]
2019-08-29 01:02:41 +00:00
satyanveshd f378b67565 [sample] add new cookbook sample - occupancy (#1352)
* occupancy.cpp with Makefile

* occupancy sample changes according tothe comments

* Changes according to the review comments

* Occupancy Sample Changes

* Changes according to review comments


[ROCm/hip commit: f807cc1a7b]
2019-08-29 01:01:49 +00:00
mshivama 37779f5bef Device side support for Cooperative Group feature (#1202)
* first cut of the header implementation of cooperative group feature

* add diclarations for device library functions

* fixed various compile time issues in the CG headers

* enabled copy construction and copy assignment

* fixed a minor bug related to conditional compilation macro

* fixed few more CG constructor issues and added a unit testcase

* fixed typo

* extended unit testcase

* compute size of partitioned CG from mask

* bit of code refactoring

* removed boilerplate code

* fixed few of the review comments by Brian

* Changes to the sigantures of few grid and multi-grid related OCKL functions

* changes to declarations of OCKL functions related to CG feature

* removed all the block level support as it is not planned for 2.9

* Have taken care of review comments by Brian

* Have taken care of review comments by Brian

* removed unused functions which were initially intended to use in block level cg support


[ROCm/hip commit: d75dc4eb29]
2019-08-29 01:01:25 +00:00
Michael LIAO e3d7baceff [hcc] Fix previous replacement of result_of_t.
- `result_of_t` is defined as the shortcut of
  ```
  template< class T >
  using result_of_t = typename result_of<T>::type;
  ```


[ROCm/hip commit: 63e47e525b]
2019-08-26 10:58:38 -04:00
ramcherukuri 8b5587cebd moving result_of_t to result_of
[ROCm/hip commit: 3a6ca29815]
2019-08-24 08:59:58 -04:00
Rahul Garg bd916675eb Make Bundled_code_header visible for hipRTC usage (#1359)
[ROCm/hip commit: 0fd14a3e13]
2019-08-23 09:20:02 +00:00
Aryan Salmanpour 0fc745b3a6 [hip] add initial implementation for hipLaunchCooperativeKernel API (#1339)
* [hip] add initial implementation for hipLaunchCooperativeKernel API

* [hip] use total number of work groups to initialize the GWS resource

* [hip] use only one argument for init_gws kernel

* [hip] use the device associated with the stream for checking the device properties


[ROCm/hip commit: 5066700ace]
2019-08-23 09:19:35 +00:00
Sarbojit2019 edb699bd32 Compilation failure on nvcc path when using hipChannelFormatKind (#1345)
Fix for github #1183 issue reported

[ROCm/hip commit: 84de192c9b]
2019-08-21 10:01:03 +00:00
kpyzhov 612833bcfe Corrected declaration of __ockl_clz_u64() (#1340)
[ROCm/hip commit: 0e3198be25]
2019-08-20 12:06:36 +00:00
Yaxun (Sam) Liu aae6ad3ab4 Fix missing decl for hip-clang
Add back decl for hipHccModuleLaunchKernel and hipExtModuleLaunchKernel for HIP/VDI only


[ROCm/hip commit: 51f0b3f3a6]
2019-08-19 18:27:13 -04:00