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

574 Коммитов

Автор SHA1 Сообщение Дата
Alex Voicu d9075301c3 This adds cursory support for globals to the HIP module loading API. The 
style is purposefully alien so as to signal that HIP experts should turn
it into HIP worthy code as soon as possible.


[ROCm/clr commit: 582779c6c6]
 2017-10-09 13:27:11 +01:00
Siu Chi Chan 063dae2c46 ensure the condition is evaluated before applying the negation operator 
[ROCm/clr commit: bf6a3f4294]
 2017-09-20 01:38:28 -04:00
Maneesh Gupta e3aa4edf79 Merge pull request #155 from wsttiger/master 
Modify hip headers such that they are more compatible with strict C compiler

[ROCm/clr commit: 01163d327b]
 2017-09-15 10:49:55 +05:30
Maneesh Gupta c443f3814f Fix typo in nvcc_detail/hip_runtime_api.h 
[ROCm/clr commit: 846b0555b9]
 2017-09-14 16:19:57 +05:30
Maneesh Gupta bb818d9c74 Merge pull request #175 from gargrahul/assert_support 
Device side assert support

[ROCm/clr commit: 096caca840]
 2017-09-14 16:08:00 +05:30
sriharikarnam f65fb4755e Add hipDevice[Get/Set]SharedMemConfig API on nvcc details 
[ROCm/clr commit: f6fda276ce]
 2017-09-14 16:03:19 +05:30
Rahul Garg 2725242ba4 Device side assert support 
[ROCm/clr commit: 9dcf2ad751]
 2017-09-07 20:45:27 +05:30
Ben Sander dcd8961a9d Update docs. 
- Review unsupported comments and refresh.
- Review experimental tag in API.


[ROCm/clr commit: a6d1778fff]
 2017-08-28 15:44:38 -05:00
wsttiger ef8c6a67fc Modify header such that it's compatible with strict C compiler 
[ROCm/clr commit: 8302138d57]
 2017-08-15 13:23:09 -05:00
wsttiger 5ba2f6ea57 Add missing CUDA tags 
[ROCm/clr commit: 7933b3292d]
 2017-08-15 13:22:20 -05:00
Siu Chi Chan 6598eabd24 implement __threadfence_system 
[ROCm/clr commit: b6e22b5c93]
 2017-08-02 08:50:18 +00:00
Ben Sander a5b3f825c2 Merge pull request #100 from weixingzhang/texture 
HIP Texture Support

[ROCm/clr commit: 702651fc85]
 2017-07-26 19:28:15 -05:00
Maneesh Gupta f29245a846 Renable frexp(f) device math function 
Change-Id: I53c022b8ddf38cd17ddb42eba457b9020db66395


[ROCm/clr commit: 1bd1c6bea8]
 2017-07-20 14:41:30 +05:30
Weixing Zhang d9abb032f7 HIP Texture Support 
[ROCm/clr commit: ccbd3b13fc]
 2017-07-17 15:16:12 -04:00
Wen-Heng (Jack) Chung 4ce97c30e9 Remove explicit address spaces declarations 
[ROCm/clr commit: 0237aeab06]
 2017-07-07 12:46:29 -05:00
Ben Sander 57733404c1 Add hipdbPrintMem - wrapper for hcc memory tracker. 
[ROCm/clr commit: 18660be8ce]
 2017-07-03 15:05:30 -05:00
Rahul Garg ce0833f3bb Fixed build error in hipDeviceGetByPCIBusId 
Change-Id: I33be362910c4c5dca7435fb9c41f427b54f0e9a7


[ROCm/clr commit: cbc98cc098]
 2017-07-01 07:56:30 +05:30
Ben Sander 35f05c0a3a Refactor hip_hcc. 
Don't require setting __HIP_PLATFORM_HCC__ ; Instead check if compiler is HCC.
The functions here use HCC-specific functionality so only work with HCC.
ANd they work regardless of the __HIP_PLATFORM_HCC__ setting so don't
require that.

Also remove the "hcc_detail" extra hierarchy level for hip_hcc.h as
it is not necessary.  Remove hcc_detail/hip_hcc.h.


[ROCm/clr commit: 5e5b017b0d]
 2017-06-30 08:26:15 -05:00
Rahul Garg 1be7dc7cc2 Fixed hipDeviceGetByPCIBusId 
Change-Id: Ia36bb9425671ef7659541c9aeedae4098456a31b


[ROCm/clr commit: 467a2ba014]
 2017-06-30 10:11:41 +05:30
Rahul Garg 8c9545ad7c Fixed hipDeviceGetPCIBusId for HIP/NVCC 
Change-Id: I662efa148257a710f09002850b41d57bef00dff3


[ROCm/clr commit: 38d48b5cf0]
 2017-06-29 00:13:02 +05:30
Rahul Garg 1ff995a92a Fixed hipDeviceGetPCIBusId for HIP/HCC 
Change-Id: I3688fa2476e1baada2d3c5fc3735cec3f15a1e21


[ROCm/clr commit: a7c727f352]
 2017-06-28 23:48:27 +05:30
Sun, Peng 8a45f03573 Remove some warning debug info and add weak attribute back to GGL __global__ define 
Change-Id: I2021b107dda697b1262d44fa1506465e94a3916b


[ROCm/clr commit: 3d2a729580]
 2017-06-27 14:15:16 -05:00
Aditya Atluri ede75a84ab fixed default args for symbol memcpy apis 
Change-Id: Ie0b63f8b9c5535eb3946bd6af3f30fe71a015244


[ROCm/clr commit: 3043766899]
 2017-06-23 19:05:44 -05:00
Ben Sander f1bed37a34 Clean up old USE_* and RELEASE.md notes. 
[ROCm/clr commit: 42882ddf9c]
 2017-06-23 18:05:30 -05:00
Rahul Garg 3e29f81050 Added device side abort function in HIP/NVCC 
Change-Id: I6ae35a72a8b9c34852619f02da1a046c8d3b2ed3


[ROCm/clr commit: 0fd6b59e22]
 2017-06-20 09:38:56 +05:30
Rahul Garg 20dd968547 Abort device function in HIP/HCC, need new HCC 
Change-Id: I4195ab75e9b7b48c8b8128d6925ddc0fa5e9e009


[ROCm/clr commit: d9935cd089]
 2017-06-18 12:31:31 +05:30
Aditya Atluri cd12c963b0 removed bad copy constructor 
Change-Id: I661991d9d43941a61848b0b8e9879c0bfa811b40


[ROCm/clr commit: 34e14bb02d]
 2017-06-16 09:02:26 -05:00
Sun, Peng a1a23c69d3 Additional GGL make_kernel_functor_* macros, contributed by Alex 
Change-Id: I01aabb7d2b5418fcefb1bbf78eb5d1888dbc5c96


[ROCm/clr commit: 9bce2af76f]
 2017-06-14 11:10:52 -05:00
Sun, Peng 14e51d052e Fix error related to undefined reference of __get_dynamicgroupbaseptr(). 
Change-Id: I14951e1725e35dd5f5e53805f81cdb58661f59f2


[ROCm/clr commit: 682dda4418]
 2017-06-08 19:24:32 -05:00
Sun, Peng 65ead764d3 Add clang version guard so the hip_fp16.h header won't be picked up by gcc 
Change-Id: Ia21335a455bc93210901b44bc8c76a7f4a385b55


[ROCm/clr commit: 5450021f93]
 2017-06-08 19:24:32 -05:00
Sun, Peng 450a26e5d4 Improve HIP kernel names, attributes and codegen, contributed by Alex Voicu 
Change-Id: I2cafbdc5a98e26c7f4fad84739c915e7dc09993c


[ROCm/clr commit: 3b6a863eef]
 2017-06-05 11:39:00 -05:00
Ben Sander 7237ed04f3 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


[ROCm/clr commit: 823281dcba]
 2017-06-05 08:50:22 -05:00
Aditya Atluri 97fa7aeef6 added half data type and vector destructors 
1. Added half data types to hip_fp16.h
2. Added destructor to vector data types

Change-Id: Id5ae76a663bb90a4bde2839ec79c58fbaee5072f


[ROCm/clr commit: fdcc223842]
 2017-06-02 11:19:33 -05:00
Evgeny Mankov afbf55a9dc [HIP] [HIPIFY] CUDA Driver API 8.0.44 JIT options support. 
[ROCm/clr commit: 463c026976]
 2017-05-31 18:55:29 +03:00
Ben Sander 0ca3262f0a Add event controls for release fences. 
Env var : HIP_EVENT_SYS_RELEASE
Event allocation flags : hipEventReleaseToDevice, hipEventReleaseToSystem
   (remove hipEventDisableSystemRelease)

Update test for new functionality.


[ROCm/clr commit: 942ec0eff8]
 2017-05-27 16:02:34 -05:00
Ben Sander 9442c6dd2d Updates so hip compiles on CUDA. 
[ROCm/clr commit: 8dc968f036]
 2017-05-27 15:55:07 -05:00
Ben Sander d302498787 Add hipHostMallocCoherent, hipHostMallocNonCoherent 
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.


[ROCm/clr commit: dda70ae514]
 2017-05-24 00:48:10 -05:00
pensun f848e9f117 fix GGL helper header file, reorder for C++17 
Change-Id: I3d9ddfe670bf7e3e8e7bd85e52cc61f48c19c213


[ROCm/clr commit: 2523f8a492]
 2017-05-22 08:52:43 -05:00
Evgeny Mankov 052f630bd3 [HIP] [HIPIFY] [FIX] cuModuleLoadDataEx -> hipModuleLoadDataEx 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/81

1.	Do not use JIT options on HCC path, call hipModuleLoadData instead.
2.	NVCC path is unchanged, to call cuModuleLoadDataEx with all options.
3.	Get rid of manual hipification, based on #ifdef #else for NVCC/HIP.
4.	Update documentation accordingly.


[ROCm/clr commit: ae9f14ef9c]
 2017-05-19 17:22:14 +03:00
Aditya Atluri 905ab9a689 fixed vector type issues by reverting to old code, changed __half2 to map to vector types in llvm 
Change-Id: I7317408c25e8c1a0c02a346042c9137e160c8bbd


[ROCm/clr commit: 0433a2e608]
 2017-05-18 10:51:07 -05:00
Aditya Atluri 0318e91450 changed vector types to make sure it generate proper llvm vector types 
Change-Id: I6c4616dae137dc4eac35e5827dc5b7f3251e0247


[ROCm/clr commit: 93fa174900]
 2017-05-16 21:35:40 -05:00
Ben Sander 4ac6ac9d1d Add initial HIP_SYNC_NULL_STREAM=0 mode. 
This eliminates host-synchronization for null stream.  Instead, the
null-stream uses GPU-side events to wait for other streams.
Default is OFF pending additional testing.

Add enhanced null-stream test.

Also refine HIP_TRACE_API.


[ROCm/clr commit: 8bc6ee5932]
 2017-05-16 19:04:25 -05:00
Rahul Garg 293524f1dc Added hipMallocPitch on HIP/NVCC path 
Change-Id: Ie3ba7d3f95acac23805efa919531043b350a3f21


[ROCm/clr commit: d22b731f95]
 2017-05-16 07:15:13 +05:30
Ben Sander 9b222c0ae4 Add hipEventDisableSystemRelease flag. 
[ROCm/clr commit: 2c2625cb9e]
 2017-05-12 16:06:03 -05:00
Aditya Atluri b5f0a9471d added guard against hip_runtime.h so that non-hcc compilers can use it 
Change-Id: I3d68deda9ce8a5956e21e15a69e549d6c21e3e39


[ROCm/clr commit: 14930dc594]
 2017-05-09 10:14:16 -05:00
Rahul Garg ba1a3360ab hipMemcpy2DAsync for HIP/NVCC 
Change-Id: I46f0057fef49bdaaac41c1df80c3e27432b8f376


[ROCm/clr commit: f77059218c]
 2017-05-04 06:47:55 +05:30
Rahul Garg 9739d5d60f Added support for hipMemcpy2DAsync in HIP/HCC 
Change-Id: Ia4a8306f2dc1e33a81a7195ec29aef652fcccc4b


[ROCm/clr commit: b136e80a45]
 2017-05-03 22:29:12 +05:30
Aditya Atluri 6dccc18fa0 fixed hipFuncSetCacheConfig on rocm path 
Change-Id: I937a3afbf115edc94a753a0beb2230ed60a6f021


[ROCm/clr commit: 208bdbbcbb]
 2017-04-28 11:53:11 -05:00
Aditya Atluri afec5e075b added hipFuncSetCacheConfig API for nvcc path 
Change-Id: I87fae35bc0e10a0dca5ae1c5015fe5d9e52a1d0d


[ROCm/clr commit: e91c35fde0]
 2017-04-26 18:56:57 -05:00
Sun, Peng a82ecbcc13 fix hip_complex.h header on NV path 
Change-Id: Ia95d003ca1b284bab1c76723050e6b3b89178f65


[ROCm/clr commit: 50daa408aa]
 2017-04-25 00:15:20 -05:00