AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
1,757 Commits 3 Branches 0 Tags
0be2d65746b2f41fb585fea41db074ed8456fc6e
Commit Graph

559 Commits

Author SHA1 Message Date
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
Ben Sander 05c136e7b8 Fix hipMalloc to return error code if allocation fails. 
[ROCm/clr commit: fb7eee01ff]
 2017-04-24 22:30:54 -05:00
Aditya Atluri 119f5a1e67 changed arguments for hipPointerGetAttributes 
Change-Id: Ia7a7c4722c1f7d0a23f0e5cc3dd6dea6c01c1fd8


[ROCm/clr commit: 85c189c846]
 2017-04-24 15:24:16 -05:00
Sun, Peng 4ac3084503 add support of hipLaunchKernelGGL on NV path 
Change-Id: I0aeafd80c2181873be385d985f1d8ed86a98d136


[ROCm/clr commit: c224209200]
 2017-04-19 11:00:25 -05:00
Sun, Peng 6a3bee59f1 fix broken header in NV path 
Change-Id: Ia3aff2a89d9ba49547f51ce03a3304dfab58ba25


[ROCm/clr commit: ee299695a8]
 2017-04-19 10:47:40 -05:00
Ben Sander ab55162481 Add integer abs (initial implementation, can be optimized with OCML) 
Change-Id: I1f568c8c0e2333af1fda4c313dc48ea0c5b6ab00


[ROCm/clr commit: 8bd34535b4]
 2017-04-11 01:16:28 +00:00
Sun, Peng a5e8222af8 Fix ifndef guard in hip_fp16.h 
Change-Id: I0215556e7aa98a74e8a984e4de3fb6e8cafdfb24


[ROCm/clr commit: 3c04722d10]
 2017-04-10 11:17:05 -05:00
Sun, Peng 588dba559c add math.h to cover sqrtf function 
Change-Id: Ia37752710cea4ca77e0a4e61f8e69a0355d9488d


[ROCm/clr commit: bfa61eac2c]
 2017-04-10 08:53:12 -05:00
Sun, Peng 4cd6fb07d5 Update the define of __global__ for GGL 
Change-Id: I563bb2a132403bcbe9e9f279b55406cf0255af7d


[ROCm/clr commit: 9884f2e83f]
 2017-04-07 16:39:33 -05:00
Sun, Peng 7cedda4996 Add more operator overloading for float2 type, contributed by Aditya 
Change-Id: If1ab7fb24d64bb5304142aed0951c9bd5ad47d20


[ROCm/clr commit: 19987ede22]
 2017-04-07 14:17:41 -05:00
Sun, Peng 9fd6c7179d update GGL to log launched kernel information 
Change-Id: Ied0aa6055673c687071b4a579aecd17f0f3f09ce


[ROCm/clr commit: f699e02715]
 2017-04-07 14:06:31 -05:00
Ben Sander dc9e957a36 Finish adding start/stop event support to hipHccModuleLaunchKernel. 
Change interface to use hipEvent_t rather than hipEvent_t*

Change-Id: I259062dc087a13d51dc27f84e1e8861f332a104d


[ROCm/clr commit: e9eaadd135]
 2017-04-06 21:02:50 -05:00
sunway513 c2acfe24cc Improve documentation for hipModuleLaunch functions. 
Change-Id: I0e22621e499775740c3301347b7416d5f98c2414


[ROCm/clr commit: fb4e2307f1]
 2017-04-06 21:02:50 -05:00
Aditya Atluri 950dfd28d6 fixed header structure for complex data types 
Change-Id: I16bf19005d933f42e8c8603c5d0b2df8ea3ad04f


[ROCm/clr commit: 1358bd8f07]
 2017-04-06 16:43:26 -05:00
Sun, Peng 9d6a04d334 GGL update, add while 0 guard for hipLaunchKernel API 
Change-Id: Ie48ef8ca2ab5e26a51febfcd92417902c33fbf66


[ROCm/clr commit: 49a38da6e3]
 2017-04-06 10:48:11 -05:00
Aditya Atluri d1c334df66 added __host__ for complex functions and corrected memset and memcpy test 
Change-Id: I9ffefb7a0025aa111a54d20d2766982df15532e7


[ROCm/clr commit: 42739c37ef]
 2017-04-06 09:29:44 -05:00