AI/rocm-systems
2
0
Fork 0
Koodi Ongelmat Pull-pyynnöt Actions Paketit Projektit Julkaisut Wiki Toiminta
1 291 Commitit 3 Branchit 0 Tagit
4ad87441392aca859949c8e413b9e91c7da1030f
Commit Graph

1291 Commitit

This Branch
This Branch
Kaikki haarat
Tekijä SHA1 Viesti Päivämäärä
Ben Sander 4ad8744139 Support size_t in memset kernel. 
Add disable for HSA_AMD_AGENT_INFO_MAX_WAVES_PER_CU
Remove one copy of completion_future in memset.


[ROCm/clr commit: fd5b0c68b1]
 2016-12-22 12:25:09 -06:00
Maneesh Gupta 861429a560 hip_hcc package changes 
- updated hip_hcc package creation dependencies
- support build hip_hcc package for HCC-1.0

Change-Id: Idf23e415eff8cb352a8906191c79bd822c7618e7


[ROCm/clr commit: 1b50462ce0]
 2016-12-22 15:30:38 +05:30
Ben Sander 693bfc85bc Increment API sequence number. 
Change name to tls_tidInfo


[ROCm/clr commit: cf338d716b]
 2016-12-21 15:30:36 -06:00
Evgeny Mankov 1292eb401c [HIPIFY] Statistics in CSV file. 
+ Stats by CUDA ref name.
+ Conversion %.

TODO: Calculation of changed code amount, based on actually replaced bytes.


[ROCm/clr commit: ac8166d051]
 2016-12-21 23:08:01 +03:00
Rahul Garg 21f10a7eae Removed redundant GetPCIBusID int version function 
Change-Id: I37f2ff87d09fcfb1e3b104c44c51f606fcb83c01


[ROCm/clr commit: 0578febb99]
 2016-12-20 23:25:16 +05:30
Evgeny Mankov 1524f73ab0 [HIPIFY] Reflect unsupported CUDA API refs in statistics 
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/53

+ Unsupported refs (by HIP) are now might be listed along with the supported ones.
+ Warnings are added for the unhandled (by HIPIFY) refs, for instance:
  "warning: the following reference is not handled: 'cublasContext' [param decl ptr]."
+ Reflect unsupported CUDA API refs in statistics.
+ Occupancy API [HIP_UNSUPPORTED].
+ A few CUBLAS refs are listed as HIP_UNSUPPORTED.

TODO: Statistics in CSV file.


[ROCm/clr commit: ea8e886077]
 2016-12-19 14:38:19 +03:00
Rahul Garg 7121e56949 Fix for HCSWAP-67 
Change-Id: I0b2ce5ab933237947fb41d89769db3da16e5be6a

Conflicts:
	src/hip_hcc.cpp


[ROCm/clr commit: 4988975b59]
 2016-12-19 16:19:51 +05:30
Ben Sander 8ab567e331 Add name for function 
[ROCm/clr commit: 5d815937de]
 2016-12-17 08:54:09 -06:00
Ben Sander c59c82916a Remove HSA dependency from hipFunction_t 
Place _groupSegmentSize and _privateSegmentSize inside Function,
remove hsa_executable_symbol_t.


[ROCm/clr commit: 2bd70ff345]
 2016-12-17 07:22:56 -06:00
Ben Sander a3064807b5 Remove USE_DISPATCH_HSA_KERNEL=0 path. 
[ROCm/clr commit: 06d382bc6d]
 2016-12-17 07:22:56 -06:00
Ben Sander 68d861e8c5 Refactor Module and Function APIs. 
- hipFunction_t is now returned by value.  This eliminates dynamic
      allocation / memory management complexity in the module.  Removed
the kernel
      name so the structure is just 16 bytes now.

    - Moved the hsa_executable_load_module and hsa_executable_freeze
      calls to the hipModuleLoad and hipModuleLoadData calls.

    - Apply sharedMemBytes in hipModuleLaunchKernel to group segment
      size (not private).


[ROCm/clr commit: 3f9404d0e1]
 2016-12-17 07:22:33 -06:00
Rahul Garg 8acb6a623d Mapped hipDevice_t to int 
Change-Id: I6cfa56c42b7cd04aa0e0bce510c0d72d34ea211a


[ROCm/clr commit: bddaa0e81c]
 2016-12-17 16:53:03 +05:30
Aditya Atluri 3e3db78eb0 disabled half native support as inline asm is not working 
Change-Id: I3073d8ae39eed321987f0f2f0e689eec4cdbb48c


[ROCm/clr commit: c673aec971]
 2016-12-16 09:24:59 -06:00
Ben Sander 1a58ccc3b4 Print limits on CUDA devices 
[ROCm/clr commit: ab07d9b4a7]
 2016-12-16 08:55:11 -06:00
Ben Sander 4d51266580 Fix typo 
[ROCm/clr commit: d39ef58daf]
 2016-12-15 14:42:52 -06:00
Ben Sander 8288cbdae4 fix copyright 
[ROCm/clr commit: b53ba931e8]
 2016-12-15 14:42:52 -06:00
Ben Sander 8353b8ed72 remove TODO file 
[ROCm/clr commit: a30b36afdc]
 2016-12-15 14:42:52 -06:00
Evgeny Mankov be8dd18914 [HIPIFY] nested macro is not hipified, when it isAnyIdentifier 
Fix for https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/55


[ROCm/clr commit: a9488603b4]
 2016-12-15 21:00:34 +03:00
Brecht Carlier bceb8949c7 Update hip_faq.md 
Fixed navigation and list.


[ROCm/clr commit: cc73dd4ed5]
 2016-12-15 14:08:34 +05:30
Martin Schleiss 23ddb5aec4 Fix another typo 
[ROCm/clr commit: 8a4fe76de2]
 2016-12-15 14:07:20 +05:30
Martin Schleiss 716fac9a99 Fix various typos 
Conflicts:
	README.md

Change-Id: Ie296d503d16121a62fed1a208352ec2b81c97fd9


[ROCm/clr commit: dc8db38f04]
 2016-12-15 14:06:38 +05:30
Peter Steinberger 432f1c2b7a Fixes a typo: perforamnce -> performance 
Change-Id: I85e3b3d22c98c16556227283bfb33530e1bce2cf


[ROCm/clr commit: e2dc1cc27f]
 2016-12-15 14:01:08 +05:30
Aditya Atluri 1844a95003 fixed compilation issues 
Change-Id: I96692538736e2e4f2da9dba9c8c29a164aec4c0d


[ROCm/clr commit: a1d1fcfdac]
 2016-12-14 16:50:16 -06:00
Aditya Atluri 657739b19f added half2 support 
Change-Id: I0f3b9b7037fed97e80ec99f5369c75a63f001aae


[ROCm/clr commit: c20a86d866]
 2016-12-14 14:18:48 -06:00
Sandeep Kumar 4d78e20eed 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


[ROCm/clr commit: 8b0ce6e81b]
 2016-12-14 16:27:14 +05:30
Aditya Atluri a86ef4e577 added simple half math ops 
Change-Id: I10b1d1023a9e5f2ba63f28c4a2bbe60ee49a8aee


[ROCm/clr commit: 01ed8e91e9]
 2016-12-13 20:20:58 -06:00
Aditya Atluri b26857a631 disabled compiler flag hcc 4.0 for half support 
Change-Id: I32175113f4c05d43310b3a05c2a14e12f6d48b09


[ROCm/clr commit: 26934a920c]
 2016-12-13 20:06:56 -06:00
Ben Sander 1f638c1da6 Add USE_IPC to disable use of IPC APIs. Set to 0. 
[ROCm/clr commit: 5eed20be12]
 2016-12-13 15:07:04 -06:00
Aditya Atluri 9691299b0d added few type reinterpret cast device functions 
1. __int_as_float
2. __hiloint2double

Change-Id: Id247c196887b24a12090f0521bf91e13afeec733


[ROCm/clr commit: 7a712aa76b]
 2016-12-13 14:41:36 -06:00
Aditya Atluri c865d93792 added half math addition ISA support 
Change-Id: I293b771f695b499b795d7e53f600c9e4fe2a2071


[ROCm/clr commit: 02eab122c5]
 2016-12-13 09:18:34 -06:00
Evgeny Mankov e22ed56bd7 [HIPIFY] Code refactoring and total stat collecting 
+ Single base class for Preprocessor and MatchFinder classes.
+ Total Stats for multiple files is added.


[ROCm/clr commit: 6bcacf83a4]
 2016-12-13 18:01:08 +03:00
Evgeny Mankov 1da43c7216 [HIPIFY] Rename -n to -examine 
[ROCm/clr commit: b73ffa4e7c]
 2016-12-12 20:03:01 +03:00
Evgeny Mankov c9aa0841d8 [HIPIFY] Multiple source files support. 
[ROCm/clr commit: d5eb7f494f]
 2016-12-12 19:57:19 +03:00
Aditya Atluri 4c61746162 Changed threadfences to match target parsing by hcc 
Change-Id: I28fcabbaacd13495b707f263fd09afaead0665fa


[ROCm/clr commit: 812cf130b6]
 2016-12-12 10:16:58 -06:00
Evgeny Mankov 131f601cf7 [HIPIFY] -no-backup option is added. 
Is useful for release hipifying in place.


[ROCm/clr commit: c5f5e662ef]
 2016-12-08 23:14:19 +03:00
Evgeny Mankov 845f7a00db [HIPIFY] -no-output support. 
Actually output file is created by clang itself, but isn't updated and is deleted after processing.
In cooperation with -print-stat -no-output (or single -n) is used for examine the source CUDA code.

Conflicting options:
-inplce
-o


[ROCm/clr commit: f5deff4ba3]
 2016-12-08 22:45:10 +03:00
Evgeny Mankov 3dcd27d0b1 Fix the limitation of supported input files. 
Actually .cu and .cuda was supported.

+ All the file names are allowed, including file names without extension.

[IMPORTANT]
To hipify CUDA input file, which name is not *.cu, please add option "-x cuda" after tool's options ending marker "--", for instance:

./hipify-clang NeuralNet -- -x cuda

This option will go to clang itself, not the hipify tool.


[ROCm/clr commit: a81dfc5a0f]
 2016-12-08 20:28:43 +03:00
Rahul Garg f45c6facf0 Fixed build error due to GetPCIBusId overloaded function 
Change-Id: I626446f2c72c8143f08c95367bc1c528abeaf69d


[ROCm/clr commit: a6b2f9c3a0]
 2016-12-08 14:35:58 +05:30
Maneesh Gupta 6fbb70b974 hcc_detail/hip_runtime_api.h: Fix IPC API signature 
Change-Id: I0be0f09c62f231620341141bd66183c3338be56a


[ROCm/clr commit: c677041b37]
 2016-12-08 12:50:25 +05:30
pensun 0d8957fb9a HIP IPC implementation on ROCr IPC APIs 
Change-Id: I1ca9d520f5d0b1b56694211471b81eb7c6c23d16


[ROCm/clr commit: 7ac5f2e8c3]
 2016-12-07 15:38:36 -06:00
Rahul Garg 89490a8065 hipDeviceGetPCIBusId int version changes for CUDA runtime API 
Change-Id: I4d3b995f1d1ac83415ca84808a074e5c8cd72f3c


[ROCm/clr commit: d8fdd6c6fc]
 2016-12-07 12:12:40 +05:30
pensun 87f69ab605 Fix issue of ihipModule_t double defined 
Change-Id: I508677e595776fd573a2f224691116d01288dc78


[ROCm/clr commit: 8f2a1752c1]
 2016-12-06 19:10:17 -06:00
pensun e885147485 change hipgetPCIID to take int as third parameter 
Change-Id: I4429b36756a6d868a769abd783bf28a55147c0d0


[ROCm/clr commit: 8fcae3acc0]
 2016-12-06 14:24:09 -06:00
pensun 707358d0b4 IPC prototyps and part of the implementation included 
Change-Id: Id88c7f155d23ec63f57a6ef05098fba43f8af336


[ROCm/clr commit: 092924d660]
 2016-12-06 14:24:09 -06:00
pensun aaecc3fe04 local changes for hipnccl 
Change-Id: I05a1f0381ce2914a800f573342cc954eb5ff82d9


[ROCm/clr commit: 808e555247]
 2016-12-06 14:22:02 -06:00
Ben Sander 448c6b3119 Enabled USE_DISPATCH_HSA_KERNEL, with serialization in hipModuleUnload. 
[ROCm/clr commit: 3f810a203b]
 2016-12-06 10:14:01 -06:00
Rahul Garg 74803e3ddf Simple test case for hipDeviceGetPCIBusId 
Change-Id: I0fb6d1bef4739a5b6280928f7b349d95c1656431


[ROCm/clr commit: afc81c955e]
 2016-12-06 17:31:54 +05:30
Rahul Garg 8a210f721d Build Error correction in hipDeviceGetPCIBusId 
Change-Id: I50ff4d95b7a732924c7a991cba60400b1c93c0de


[ROCm/clr commit: a019f1ce39]
 2016-12-06 17:09:21 +05:30
Rahul Garg 48e9aaf696 Changed hipDeviceGetPCIBusId to return Bus ID as string 
Change-Id: I6d5aa7362084109d34bc015d948f8723b2a38ee9


[ROCm/clr commit: 0017419521]
 2016-12-06 16:55:17 +05:30
Maneesh Gupta b9bde4a4be Remove redundant variable g_malloc_heap_size 
Change-Id: Idaf47be70488f0deb3eab05a86d9c5a413d3fff7


[ROCm/clr commit: b8413a69c8]
 2016-12-06 10:19:03 +05:30