AI/rocm-systems
2
0
Fork 0
Código Incidencias Pull Requests Acciones Paquetes Proyectos Lanzamientos Wiki Actividad
124 Commits 3 Ramas 0 Etiquetas
8bc80debe45e5442740cfb2d2b79bc1d43deecff
Gráfico de commits

108 Commits

Autor SHA1 Mensaje Fecha
Aditya Atluri 8bc80debe4 Fixed bit_extract 
Change-Id: I92d7b7a302e3fa0db84889fb5dc6b612e6a53c73
 2017-03-31 13:35:26 -05:00
Aditya Atluri 7735b454a1 added new api hipHccModuleLaunchKernel 
1. hipHccModuleLaunchKernel is same as hipModuleLaunchKernel with OpenCL workitem model
2. Added copy right
3. Fixed header naming

Change-Id: I6a7c35a3566e2f8d3f5056613e34193775d4b236
 2017-03-31 12:11:34 -05:00
Sun, Peng c4c4d95db6 revert workaround for square sample and update doc on GGL 
Change-Id: I731c68ca4111e7dc2e45bef51c4cad2c23fc81f8
 2017-03-21 10:26:09 -05:00
pensun 323807d02b Initial integration with Alex' Generic Grid Launch 
Change-Id: I559afb80e9e39ec0d119bb3bf3b85ef9e448caf6
 2017-03-17 14:59:34 -05:00
Aditya Atluri 219343027f Added default module launch api functionality 
1. As in hipModuleLaunchKernel(..., kernelParams, nullptr); works with this commit
    2. Added headers AMDGPUPTNote.h, AMDGPURuntimeMetadata.h to do code object meta data parsing
    3. Changed CMake to look at llvm link libraries
    4. HIP developer should set env variable LLVM_HOME to remove link errors
    5. HIP depends on installed LLVM (not source, not build)
    6. Added sample to test out the feature
    7. Right now HCC does not support embedding metadata in code object. Use clang opencl
    8. Changed HIPCC to read LLVM_HOME env var
    9. New argument to CMake should be given -DLLVM_HOME=<where llvm 5.0 is installed>

Change-Id: Iba38194aa872d97cc2c90a8e5ff746c48055c868
 2017-03-17 13:11:34 -05:00
Maneesh Gupta 8d6cb1f5a3 4_shfl and 5_2dshfl samples are unsupported on gfx701 
Change-Id: I81eb880350f25e89573ba14c62b549c6c43f8c91
 2017-03-14 15:56:18 +05:30
Ben Sander 705ab93664 Refactor registered memory calls. 2017-03-11 09:18:27 -06:00
Ben Sander b25691cb87 Add first step to a "registerd" mode in hipBusBandwidth. 2017-03-11 09:18:27 -06:00
Rahul Garg 5eb39f1c6b Fix for HCSWAP-128, make 5_2dshfl cookbook sample only for fiji 
Change-Id: I8869c28151bca1bd47a053a2808e93a801d16d00
 2017-03-10 10:29:52 +05:30
Aditya Atluri a8fb90d9a9 make 4_shfl cookbook sample only for fiji 
1. __shfl is not supported on hawaii gfx701

Change-Id: Iac09f5d30ee0674b8f58a6e74ec5c49b02be32ad
 2017-03-09 08:52:50 -06:00
Aditya Atluri af22699ec6 added new field to hipDeviceProp_t structure gcnArch. 
1. It is an integer containing gfx values 701, 801, 802, 803
2. On NV path, it is zero

Change-Id: I2b4c7f48981d0214d8c6b1905d2cc85b16203419
 2017-03-07 11:24:32 -06:00
Aditya Atluri b5e3f59377 removed hipblas samples as it is not yet supported 
Change-Id: I354b710e652ce0d0413d670530ceb8b70f4993d5
 2017-02-17 08:51:02 -06:00
Rahul Garg dc2f5fcc7d Command scripts for latency measurements 
Change-Id: I8c28765a09fb0358447367939de524b12699a317
 2017-02-07 15:03:46 +05:30
Ben Sander 0390b12175 Doc update - describe debug techniques 
Also tweak sample to remove unneeded HIP_KERNEL_NAME.
Comment update
 2017-01-19 12:40:45 -06:00
Rahul Garg ba8fe1675f Fixed hipcommander default execution for HCSWAP-106 
Change-Id: I9fbd10dfaeeb4928b2ec23ceed131b5200a658f9
 2017-01-19 15:04:32 +05:30
Ben Sander cee24a20f2 Print limits on CUDA devices 2016-12-16 08:55:11 -06:00
Ben Sander 054fc61f6e remove TODO file 2016-12-15 14:42:52 -06:00
Sandeep Kumar 70716bee42 Fixes in Makefile of couple of samples 
- modified Makefile for hipblas_saxpy to replaced hcblas.so with hipblas.so as part of HCSWAP-100
- Resolved missing separator issue in peer2peer cookbook Makefile

Change-Id: I678fea267eee1481f02da09379339ed78d3f95f2
 2016-12-14 16:27:14 +05:30
Ben Sander c590cd6865 Add more debug info 2016-11-26 08:56:02 -06:00
Sandeep Kumar 5e86e5f565 fix_format 
Change-Id: I34e265de434263a11654e5deba044c3f21e86578
 2016-11-18 14:34:14 +05:30
Sandeep Kumar 8829e2626c Add p2p for cookbook 
Change-Id: Id2e77ab31123ef95885d665efe34bc0d4596733a
(cherry picked from commit 6fbd0352713ca36e399b1ed4f17c486207a53875)
 2016-11-14 06:10:36 +05:30
Maneesh Gupta aaf1547bff hcc_dialects/Makefile: use clamp-config 
Change-Id: I86df82f75b75125825e22d0545209a19386d9936
 2016-11-10 11:31:50 +05:30
Ben Sander 997dbf0d6a Update gitignore for some common output files 
Change-Id: I9cd60f042af4dba07fe0fdbd2ee442936ff8c7bd
 2016-11-06 04:26:15 -06:00
Ben Sander ab73e76987 Print non-peers too 
Change-Id: I2a6905edcdf144aa732ae3120c17780477f232ac
 2016-11-04 06:34:07 -05:00
Ben Sander b5b7663c51 Add initial hipProfileStart/Stop 
And modify sample to show how to use.
Still needs some work to understand interaction with CXL.

Change-Id: I2579824d2dd7863ea23874d34f0dabb3cb305d3e
 2016-10-27 23:09:32 -05:00
Ben Sander e2fbab109d show how to use variety of HIP_PROFILE features 
Change-Id: I6edd66ac4c068b64e1dc3787d7f1f69ab3238469
 2016-10-27 23:09:32 -05:00
Ben Sander f8c4fa982a Add new hipdemangleatp and snapshot sample update for new functionality 
Change-Id: Ie19c683b2b0bdfeb0c3fcf89444c2e21b7f606e7
 2016-10-27 23:09:31 -05:00
Ben Sander 23dc2f02cd Rename HIP_ATP_MARKER and profiling vars 
HIP_PROFILE_API
HIP_DB_START_API
HIP_DB_STOP_API

Change-Id: I6c4da67212ff8217e6356a2622d4c6278a188c34
 2016-10-27 23:09:31 -05:00
Sandeep Kumar 04af19866f Add more apps to 2_Cookbook 
Change-Id: Iafe462df9726a32f450bd240a2de3eaa73a10057
 2016-10-19 12:58:16 -04:00
Maneesh Gupta a46e251daf samples: Updated copyright header 
Change-Id: I821f514ced5e34d492cb167b65d7273e26ed7b84
 2016-10-15 23:05:04 +05:30
Ben Sander 116400c18a Refactor module API test. 
- Add PASSED/FAIL indication.
- Set args using struct rather than void* array.

Change-Id: Ic924f88c49cc46979b12b7fef8650081e3b5f58c
 2016-10-14 23:19:25 -05:00
Aditya Atluri 435c13ef7d indent correction for square.cu 
Change-Id: I2ca008e260b920ac3a503ad2a4bb28cd32300c98
 2016-10-12 19:26:59 -05:00
Aditya Atluri 1eb1c6573f added copyright to module sample kernel file 
Change-Id: If57e0761df63c902e1677084ff85106ec49df5de
 2016-10-12 19:23:48 -05:00
Maneesh Gupta 1ec9ecbf9c clang-hipify -> hipify-clang in documentation 
Change-Id: I86ebc8112477db0d3e09f240beb3f9222d909ee6
 2016-10-05 23:07:14 +05:30
Maneesh Gupta 937c0389cb samples: Updated to use new hip include path 
Change-Id: I53a1385a17f13a997ea21d14315f15a3ad851dab
 2016-10-04 22:21:10 +05:30
Ben Sander d25f665837 small typo fix 
Change-Id: I01906b330be8e6ec149bcdfe82def73e15931c89
 2016-10-02 05:57:02 -05:00
sandeep kumar db7e460626 Add 2_Cookbook 
Change-Id: I10bbbd4bcb80a5900fe6af466c8f4c94ea5efe9a
 2016-09-30 12:52:06 +05:30
Ben Sander 14ad755612 Small tool, doc, sample enhancements. 
- Expand message when HIP version mismatch detected.
- Doc touchup.
- change sorting of hipBusBandwidth so byte results shown at top.
-

Change-Id: Ifb4e44a5fdfb65d59c4994b11e5f13385705f7e0
 2016-09-26 16:36:01 -05:00
Ben Sander fdb4ed3c5e Sample improvements. 
- Enable -O3 for hipDispatchLatency.
- Use nearly-null kernel to prevent it from being optimized away.
- Formatting for hipDispatchLatency.
- Formatting for hipInfo.
 2016-09-22 13:05:47 -05:00
Aditya Atluri be3fd69bd1 added vimrc for current project 
1. Added vimrc config file for HIP
2. Corrected square sample indent

Change-Id: I3e1d92403571148fe6825db6ad63ad925ae69519
 2016-09-15 11:40:17 -05:00
Maneesh Gupta 2145e2ba61 module_api/Makefile: Update as per newer hipgenisa.sh 
Change-Id: I479c74eae00d7521434f2740ce5930e326ea05cf
 2016-09-06 17:47:10 +05:30
Maneesh Gupta e2469d5c55 module_api sample: Remove unnecessary platform checks 
Change-Id: I1d531264d51ff952a3a68d554672b6d293e23379
 2016-09-04 21:25:14 +05:30
Rahul Garg 71736d2ed2 Removed NVCC check for hipCtxXXX functions in module_api/runKernel.cpp 
Change-Id: I2bdd4fadf41063ec60626f1850e16f8307ebe6b5
 2016-09-04 20:37:29 +05:30
Maneesh Gupta b250c5a7b3 module_api: HCC path no longer needs mangled kernel name 
Change-Id: I4c1cb218bfdd05c9fba57276167e3e4205b93614
 2016-09-04 16:26:16 +05:30
Maneesh Gupta c63944fc08 module_api sample: no longer need EXTERN_C workaround 
Change-Id: Ida087d832df8e1f3620b38f920ec2853aad641c8
 2016-09-04 13:49:43 +05:30
Maneesh Gupta 6618c010b5 module_api: workaround to use vcpy_kernel.cpp for NV path 
Change-Id: Ib4868bf02c64070e846c19427c39289609909466
 2016-09-04 12:35:08 +05:30
pensun 49971e8c9e For module_api sample, use vcpy_kernel.cu to generate ptx file for NV path. 
Change-Id: Id0033678834288c4eaa56b12e7d447119be99deb
 2016-09-03 21:06:58 -05:00
Aditya Atluri 6ca7a87e0e corrected offline kernel compilation on hipcc path 
1. hipgenisa.sh now adds int main(){} during kernel compilation. User does not have to put it there
2. Renamed vcpy_isa.cpp to vcpy_kernel.cpp
3. Removed vcpy_isa.cu as the kernel code should be common for both paths
4. Changed Makefile and runkernel.cpp to work with above changes

Change-Id: I9f8c84706b44bb500bc493a68e959762b55a0142
 2016-09-02 13:17:17 -05:00
Ben Sander 512ff8ec8e Fix double-lock of stream on hipModuleLaunchKernel 
Change-Id: I4ca164971c25f4eb8fbcca11d6258367bb3d2ab4
 2016-09-02 12:47:49 -05:00
Ben Sander cb539b227c Fix av::copy in dialects to use capture-by-value 
Change-Id: Ibce1488a1326f66b92b4d5b351230666b691ed31
 2016-09-02 09:46:59 -05:00