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

1628 کامیت‌ها

مولف SHA1 پیام تاریخ
Sandeep Kumar 96a7f1853e Add inline asm hip directed tests for v_add and v_mac 
Change-Id: Ie5ace2e42d5da89b16e040537df2bb13d3883c6d


[ROCm/hip commit: 830f2b100d]
 2017-05-31 09:25:40 +05:30
Sandeep Kumar 1859451523 Add unroll and inline asm cookbook samples 
Change-Id: Ie5a0fbb01b7fca82959090d89299533d49e092f1


[ROCm/hip commit: e4f0b28bb9]
 2017-05-31 09:25:35 +05:30
Sandeep Kumar a28399f456 Print msg for single gpu 
Change-Id: I2d23c73542add8973990ba96592016726994422e


[ROCm/hip commit: dfcba01db6]
 2017-05-31 09:25:17 +05:30
Ben Sander 59833bea80 Set event->_stream on hipHccModuleLaunchKernel path if start/stop used 
Ensure _stream is always non-null in recorded events.
Fixes isDefaultStream fault.


[ROCm/hip commit: cb60763737]
 2017-05-30 21:55:46 -05:00
Evgeny Mankov f99ab93b61 [HIPIFY] Add the rest CUDA Runtime API 8.0.44 Data structures. 
+ sync with corresponding CUDA Driver API Data structures.

P.S.
There is no any new changes in CUDA Runtime API 8.0.61 Data structures since 8.0.44.


[ROCm/hip commit: 063539308e]
 2017-05-30 19:45:59 +03:00
Evgeny Mankov 8a05cf882f [HIPIFY] Add the rest CUDA Driver API 8.0.44 Data structures. 
+ Memory advise values
+ Memory Range Attributes
+ P2P Attributes

P.S.
There is no any new changes in CUDA Driver API 8.0.61 Data structures since 8.0.44.


[ROCm/hip commit: 1cc5f42e34]
 2017-05-30 18:29:14 +03:00
Evgeny Mankov 8574437d36 [HIPIFY] Add more CUDA Driver API 8.0.44 Data structures. 
[ROCm/hip commit: 3e99bc23e7]
 2017-05-30 17:58:13 +03:00
Maneesh Gupta 56bf96c6df Disable normcdfinvf on __host__ 
Change-Id: If7bfc9826a09eb9b7675ea2a417b9418759b7912


[ROCm/hip commit: 4ff01c971f]
 2017-05-30 15:45:22 +05:30
Ben Sander b3e01ed74f 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/hip commit: ec7102f461]
 2017-05-27 16:02:34 -05:00
Ben Sander e24627aa80 Cleanup hipEvent. (Intermediate checkpoint) 
Support hipEventDisableSystemRelease flag.
Update test.
Remove stray printf


[ROCm/hip commit: 620eb30691]
 2017-05-27 16:02:34 -05:00
Ben Sander c88190d698 Updates so hip compiles on CUDA. 
[ROCm/hip commit: be8d0ba644]
 2017-05-27 15:55:07 -05:00
Ben Sander 715aeef97c Add isDefaultStream() accessor. 
Fix code that checked for stream==nullptr after stream had been
resolved to a "true stream".


[ROCm/hip commit: b251d72917]
 2017-05-26 13:46:48 -05:00
Siu Chi Chan ef1a8c2788 fix hip_fast_dsqrt* to call a double fp sqrt function 
[ROCm/hip commit: 1dce01f9bb]
 2017-05-25 23:15:30 -04:00
Evgeny Mankov bc9b970f82 [FIX] [HIPIFY] Add matchers for function return types. 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/73

Examples (https://github.com/thrust/thrust/blob/master/thrust/system/cuda/detail/trivial_copy.inl):

template<typename System1,
         typename System2>
cudaStream_t cuda_memcpy_stream(const thrust::cpp::execution_policy<System1> &,
                                const thrust::cuda::execution_policy<System2> &exec)

template<typename System1,
         typename System2>
cudaMemcpyKind cuda_memcpy_kind(const thrust::cuda::execution_policy<System1> &,
                                const thrust::cpp::execution_policy<System2> &)


[ROCm/hip commit: c863215611]
 2017-05-24 18:25:40 +03:00
Ben Sander b7b7c7b7ac Remove HIP_NUM_KERNELS_INFLIGHT. (redundant with HCC controls) 
[ROCm/hip commit: 578d430bb3]
 2017-05-24 01:03:28 -05:00
Ben Sander 5b9ce41633 Add hipHostMallocCoherent, hipHostMallocNonCoherent 
Provide per-allocation control over coherent/non-coherent mem.
These overrid the default HIP_COHERENT_HOST_ALLOC setting.


[ROCm/hip commit: 75f691ec2f]
 2017-05-24 00:48:10 -05:00
Ben Sander 07865c3a02 Remove HIP_MAX_QUEUES (replaced with HCC_MAX_QUEUES) 
[ROCm/hip commit: d0ef9d8462]
 2017-05-23 23:48:01 -05:00
Ben Sander 247c34195f Expand test to cover copy followed by event sync 
[ROCm/hip commit: 236ce70e94]
 2017-05-23 23:15:45 -05:00
Ben Sander 97bdbe6590 Use accelerator_scope for create_marker and create_blocking_marker. 
As optimization when system-scope is not needed.


[ROCm/hip commit: 2b253a48b6]
 2017-05-23 23:15:45 -05:00
Ben Sander 1e0046f737 Fix trace category for hipHostMalloc 
[ROCm/hip commit: 7cfe07cff4]
 2017-05-23 23:15:45 -05:00
Evgeny Mankov 0a43773e0d [FIX] [HIPIFY] Matcher for new operator is missing. 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/80

Example from CUDA 8.0.44 sample (CUDASamples\0_Simple\matrixMulDrv\matrixMulDrv.cpp):
    CUjit_option *jitOptions = new CUjit_option[jitNumOptions];
where CUjit_option is enum, should be:
    hipJitOption *jitOptions = new hipJitOption[jitNumOptions];


[ROCm/hip commit: 3d973dc4da]
 2017-05-23 19:45:38 +03:00
Aditya Atluri 6e117234bf fixed erfinv build error as it is implemented in hcc 
Change-Id: I27a512147c53f658a63fdf3e90f5e9cfac09ada8


[ROCm/hip commit: 0559fc69e9]
 2017-05-23 09:32:19 -05:00
pensun b19e862dc4 fix GGL helper header file, reorder for C++17 
Change-Id: I3d9ddfe670bf7e3e8e7bd85e52cc61f48c19c213


[ROCm/hip commit: 6d0f58b939]
 2017-05-22 08:52:43 -05:00
Evgeny Mankov cb7e073c42 [HIPIFY] [FIX] [HIPIFY] Matcher for pointer to enum var declaration is missing. 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/79

Example from CUDA 8.0.44 sample (CUDASamples\0_Simple\matrixMulDrv\matrixMulDrv.cpp):
    CUjit_option *jitOptions = new CUjit_option[jitNumOptions];
where CUjit_option is enum, should be:
    hipJitOption *jitOptions = new hipJitOption[jitNumOptions];

[TODO]
1. new CUjit_option -> new hipJitOption.
   Matcher for new operator is missing:
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/79
2. Merge matchers cudaEnumDecl and cudaEnumVarPtr.


[ROCm/hip commit: b5a1d47e68]
 2017-05-19 17:39:09 +03:00
Evgeny Mankov 042de3e175 [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/hip commit: 270f643c9c]
 2017-05-19 17:22:14 +03:00
Aditya Atluri 721cb0f7db fixed vector type issues by reverting to old code, changed __half2 to map to vector types in llvm 
Change-Id: I7317408c25e8c1a0c02a346042c9137e160c8bbd


[ROCm/hip commit: bdc08fcf10]
 2017-05-18 10:51:07 -05:00
Ben Sander 324dfb870f Return precise address for hipHostGetDevicePointer. 
[ROCm/hip commit: 46030bb2d2]
 2017-05-17 07:36:06 -05:00
Aditya Atluri 4dbebe0409 changed vector types to make sure it generate proper llvm vector types 
Change-Id: I6c4616dae137dc4eac35e5827dc5b7f3251e0247


[ROCm/hip commit: 9dceccf136]
 2017-05-16 21:35:40 -05:00
Ben Sander bd7a374f20 Make hipMultiThreadStreams1 test a little harsher. 
Fail faster if synchronization rules are violated.
Run vectorAddRevers to read last elements of array first - if the
vector add kernel starts before preceding copy finishes we
will read stale data and flag the error.

Increase default array sizes, so synchronization errors more easily
exposed.


[ROCm/hip commit: 2e1fec47ab]
 2017-05-16 19:04:25 -05:00
Ben Sander f3dcff0906 Fix HIP_TRACE_API so kernel launch only printed when requested. 
[ROCm/hip commit: 427f8472aa]
 2017-05-16 19:04:25 -05:00
Ben Sander a55ce5bee4 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/hip commit: 27877f8854]
 2017-05-16 19:04:25 -05:00
Ben Sander cfe81dfbf4 Update tests README 
[ROCm/hip commit: c67b828a5a]
 2017-05-16 19:04:25 -05:00
Ben Sander 3107e70ea2 Doc update - split hip_debugging.md into separate file. 
[ROCm/hip commit: 704ba30b32]
 2017-05-16 19:04:25 -05:00
Ben Sander 7d07d804d8 split debugging into separate .md file 
[ROCm/hip commit: db097ab392]
 2017-05-16 19:04:25 -05:00
Ben Sander 2cf05ad54b Add HIP_TRACE_API=4. Only display memory allocation/free apis. 
[ROCm/hip commit: 0edab14139]
 2017-05-16 19:04:25 -05:00
emankov dce8786e26 [HIPIFY] *.inl extension support for batch processing 
[ROCm/hip commit: 30000ef130]
 2017-05-16 19:52:39 +03:00
Evgeny Mankov 1a183a71a5 [HIPIFY] cudaMallocPitch -> hipMallocPitch 
[ROCm/hip commit: 12d8c53c90]
 2017-05-16 18:21:25 +03:00
Rahul Garg c6a2d65d5e Added hipMallocPitch on HIP/NVCC path 
Change-Id: Ie3ba7d3f95acac23805efa919531043b350a3f21


[ROCm/hip commit: 1223612331]
 2017-05-16 07:15:13 +05:30
Evgeny Mankov 6b76c979ce [HIPIFY] CUDA Driver API: Primary Context Management support. 
[ROCm/hip commit: a97cb6810c]
 2017-05-15 15:35:52 +03:00
Aditya Atluri 62e5cda4af added gfx900 to hipDeviceProp_t 
Change-Id: I49e7a32f218926fd55f1c94c5dc2366d6c8ac4ca


[ROCm/hip commit: a43149135e]
 2017-05-12 21:43:34 -05:00
Ben Sander be423aa034 Remove old USE_ switches no longer needed. 
[ROCm/hip commit: 0679831384]
 2017-05-12 16:06:03 -05:00
Ben Sander b1b71c4c75 Add hipEventDisableSystemRelease flag. 
[ROCm/hip commit: b306095ac2]
 2017-05-12 16:06:03 -05:00
Evgeny Mankov 3408458f9f [HIPIFY] Fix string routines. 
Some Clang tooling functions return std::string, some return StringRef. Assigning of returning std::string to StringRef variables leads to garbage in it.
DEBUG build is always affected.


[ROCm/hip commit: 25d470c380]
 2017-05-11 21:50:36 +03:00
Ben Sander ff72a701b7 hipHostMalloc allocation are mapped to all devices by default. 
Support hipHostMallocPortable flag.
Default flags are hipHostMallocPortable | hipHostMallocMapped.

Also:
-refactor tests to move addCount and addCountReverse into HipTest
namespace.
-test multi-GPU host memory.


[ROCm/hip commit: c3ccaa01e5]
 2017-05-10 17:34:36 -05:00
Ben Sander 5d558861c2 Fix hipStreamWaitEvent for single GPU. 
[ROCm/hip commit: e0c3ea15b2]
 2017-05-10 13:23:49 -05:00
Aditya Atluri bdce32238f added guard against hip_runtime.h so that non-hcc compilers can use it 
Change-Id: I3d68deda9ce8a5956e21e15a69e549d6c21e3e39


[ROCm/hip commit: a38e36ec2f]
 2017-05-09 10:14:16 -05:00
Ben Sander ef98415d0e Fix some typos, add additional guidance for -BSymbolic 
[ROCm/hip commit: 687809104b]
 2017-05-05 17:29:04 -05:00
Ben Sander 639d152ff8 Refactor hipHostRegister test. 
Run all tests in one command.
Run 128 offsets.


[ROCm/hip commit: 6437f5d2b2]
 2017-05-05 17:29:04 -05:00
Ben Sander 2e2c773643 Update streamEventTEst. 
- add checks for events across devices.
- refactor test to make sure it runs long enough to sensitive sync
  techniques.
- add tests for DeviceSync, streamWaitEvent.


[ROCm/hip commit: 2d0f509de5]
 2017-05-05 17:29:04 -05:00
wsttiger 3bf30acbd7 Improve hipStreamWaitEvent test. 
- use addOne kernel, use local initializer rather than init_array.
- use addOneReverse test to add from back of array.  Test alternate fwd and backward to stress dependency logic.
- check device-side dependencies.


[ROCm/hip commit: 2a253680da]
 2017-05-05 17:29:04 -05:00