Граф коммитов

1403 Коммитов

Автор SHA1 Сообщение Дата
Maneesh Gupta 045c76a97d directed tests no longer run in an subdirectory
- target "make test" will no longer build and run tests. It will only run the tests.
- added new target "make check" which will build and run the tests.
- target "make check" will build tests serially. Use -j<N> to build tests in parallel.

Change-Id: I24c7932bf9798364a59f44631fbabcf9a5da5e17


[ROCm/clr commit: fe01dd74a2]
2017-02-27 13:14:08 +05:30
Maneesh Gupta f109c9e6da FindHIP: added new macro HIP_RESET_FLAGS
Change-Id: I0af491f6689abf1c1b5691261fe1f3e61a5d916d


[ROCm/clr commit: 58272083dd]
2017-02-27 13:11:11 +05:30
Aditya Atluri 78f1d54ad6 Added initial support for hipMemcpyFromSymbol. But not working!
Change-Id: I48d8c7de4ec9f85c6c942be995fb488a3931f5d7


[ROCm/clr commit: 7ac5017cb9]
2017-02-23 11:29:06 -06:00
Maneesh Gupta affb657bca Fix export interfaces in hip-config.cmake
Change-Id: Ifad4661ab17d7e6edb6ab300f1e92552ed917950


[ROCm/clr commit: d193187601]
2017-02-23 11:18:06 +05:30
Aditya Atluri 945526cf77 added runtime api hipMemcpyFromSymbolAsync
Change-Id: Ibaf925faf0ba464dd0ed6c5ea74c224c2ce38889


[ROCm/clr commit: 3d348b2d81]
2017-02-22 19:16:35 -06:00
Aditya Atluri 94f0fdfc5b Enable symbol tests
Change-Id: I6bd036bf00c8051c8ff728ee60562c4ebd222160


[ROCm/clr commit: 2e3f3c7d26]
2017-02-22 13:42:03 -06:00
Paul e4306010b8 Update for lower case hip
[ROCm/clr commit: 7e3a2bc1eb]
2017-02-22 15:18:38 +05:30
Paul e105026042 Change order of find_dependency
[ROCm/clr commit: 2f34d211b1]
2017-02-22 15:18:11 +05:30
Aditya Atluri 8078d7d4cc added typedef for half and half2
Change-Id: Ic844fa31b64a0354484b418df71869c2807200cc


[ROCm/clr commit: 4ef664a633]
2017-02-21 14:44:37 -06:00
Evgeny Mankov 241bd38256 [HIP] annotation update.
cudaStreamAddCallback and cudaStreamWaitEvent were excluded from unsupported.


[ROCm/clr commit: 839927a94a]
2017-02-20 21:26:40 +03:00
Evgeny Mankov 8a25b2e284 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
cudaDeviceGetPCIBusId -> hipDeviceGetPCIBusId


[ROCm/clr commit: 45f6b10459]
2017-02-20 21:21:47 +03:00
Evgeny Mankov 2d9ccb42e0 [HIPIFY] sync with HIP by HIP_UNSUPPORTED Runtime functions.
[ROCm/clr commit: eae27590d7]
2017-02-20 21:19:34 +03:00
Evgeny Mankov 45846037b1 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
Section "20. Data types used by CUDA Runtime API and supported by HIP" is added.

+ 44 supported data types are added
- 46 at least to support

All the supported data types are also supported by hipify-clang (synced).


[ROCm/clr commit: 2fb5ef1545]
2017-02-20 18:32:54 +03:00
Evgeny Mankov d85bc25d6e [HIPIFY] Sync HIPIFY with HIP by data types.
[ROCm/clr commit: d6c01aabab]
2017-02-20 18:28:59 +03:00
Evgeny Mankov 6449bad064 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
Move hipBindTexture and hipUnbindTexture to "18. C++ API Routines" from "13. Texture Reference Management". They are C++, not C.


[ROCm/clr commit: ce245f14e8]
2017-02-17 18:09:08 +03:00
Evgeny Mankov f8f5b51164 [HIP] [DOC] Update CUDA_Runtime_API_functions_supported_by_HIP
+ 21 supported functions
- 99 at least to support

All the supported functions are also supported by hipify-clang (synced).


[ROCm/clr commit: ce664e2418]
2017-02-17 18:06:47 +03:00
Aditya Atluri 810afc2a36 removed hipblas samples as it is not yet supported
Change-Id: I354b710e652ce0d0413d670530ceb8b70f4993d5


[ROCm/clr commit: 56744c0730]
2017-02-17 08:51:02 -06:00
Evgeny Mankov 19397d7e3f [HIPIFY] Add more Stream and Occupancy functions.
[ROCm/clr commit: 77e97627da]
2017-02-17 15:04:15 +03:00
Evgeny Mankov 37591af99d [HIPIFY] Add missing Memcpy functions.
+ cudaChooseDevice


[ROCm/clr commit: 72a9df0250]
2017-02-16 23:03:01 +03:00
Evgeny Mankov d2029c09db [HIPIFY] Add more Memory Management functions
[ROCm/clr commit: f37343267a]
2017-02-16 21:26:44 +03:00
Evgeny Mankov 69825b7771 [HIPIFY] Add Channel (Textures) support.
[ROCm/clr commit: 069bb1389c]
2017-02-16 21:10:10 +03:00
Evgeny Mankov c991d7c41e [HIPIFY] Add Inter-Process Communications (IPC) support.
[ROCm/clr commit: fd5d8c2bb5]
2017-02-16 20:24:53 +03:00
Evgeny Mankov f55a4f487c [HIPIFY] Add CUDA Driver LAUNCH_PARAM defines.
[ROCm/clr commit: 8a2748e8de]
2017-02-16 20:00:36 +03:00
Evgeny Mankov f98dec3bc1 [HIPIFY] Add safe type check for cudaChooseDevice matcher.
[ROCm/clr commit: d713349872]
2017-02-16 19:38:35 +03:00
Siu Chi Chan 652f3e01bb Squashed commit of the following:
commit 931d3de6c1c903cfd47842bc5026a9294ac492b4
Author: Siu Chi Chan <siuchi.chan@amd.com>
Date:   Mon Feb 13 10:54:06 2017 -0500

    only force to libstdc++ if the g++ is older than version 5 since hcc already defaults to libstdc++ with newer g++

commit 1ef8d71aa788de7b9eead4906fe56186f06d7d3f
Author: scchan <siuchi.chan@amd.com>
Date:   Sun Feb 12 14:44:11 2017 -0500

    remove hardcoded -lc++ in tests

commit 5d99ef338eb3a66523cc9ddd139e86c6fd707b9c
Author: scchan <siuchi.chan@amd.com>
Date:   Sun Feb 12 14:35:46 2017 -0500

    force include libstdc++ headers and stdc++ only if g++ version < 5 since hcc uses libstdc++ by default if g++ > 5 is present

commit a2bc21b24d100feefe91cd3cb2271238bda0738a
Author: scchan <siuchi.chan@amd.com>
Date:   Fri Feb 10 04:36:27 2017 -0500

    use hcc-config to generate compiler and linker flags

Change-Id: I13a79629c0adfd75439a47d0488ff4fd619c55ba
(cherry picked from commit 866e744e40cf1378af8a679b54959bf5226c340f)


[ROCm/clr commit: ca8045e6e4]
2017-02-16 13:12:32 +05:30
Evgeny Mankov b979de6ba7 [HIPIFY] [Fix] Crash on thrust example fallback_allocator.cu.
https://github.com/GPUOpen-ProfessionalCompute-Tools/HIP/issues/65

[Bug]
Access violation in cudaStructVar matcher.

      StringRef name = structVar->getType()
        ->getAsStructureType()
        ->getDecl() // <--- Access Violation
        ->getNameAsString();

[Solution]
Add isStructureType() check before getting type as Struct.

[ToDo]
Find case-studies for that StructVar matcher with types other than Struct.


[ROCm/clr commit: 7c1deb6140]
2017-02-15 19:48:31 +03:00
Evgeny Mankov 707099d957 [HIPIFY] Add file:line:col info to [HIPIFY] warnings/errors.
[ROCm/clr commit: 26dc7a0995]
2017-02-14 21:36:49 +03:00
scchan 5b1cb0b1c6 calls isfinite,isinf,isnan from the std namespace on the host
Change-Id: Ica2370075b89713eecfd96102e2f4e0ab9961ce4


[ROCm/clr commit: a6ac4e7097]
2017-02-14 11:52:09 -05:00
Evgeny Mankov fda8416aff [HIPIFY] Add more unhandled refs for opaque pointers.
CUfunc_st -> hipFunction_t *
CUctx_st -> hipCtx_t *
CUmod_st -> hipModule_t *


[ROCm/clr commit: 353f5b238a]
2017-02-14 17:34:10 +03:00
Evgeny Mankov 275bafea76 [HIPIFY] Fix warnings on unhandled refs.
CUstream_st -> hipStream_t *
CUevent_st -> hipEvent_t * (fixed, was -> hipEvent_t)

Warning:
[HIPIFY] warning: the following reference is not handled: 'CUstream_st' [struct var ptr]. (thrust/examples/cuda/async_reduce.cu)


[ROCm/clr commit: ce2daa53fb]
2017-02-14 17:23:09 +03:00
Evgeny Mankov b40a8f54c5 [HIPIFY] Narrow cudaKernelCallExpr matcher.
[Explanation]
Narrow cudaKernelCallExpr matcher to isExpansionInMainFile() - to the file being actually converted (without system includes).
But as for Thrust, there are *.inl files, which are nevertheless being expanded in main file.
These files contain cuda kernel launches, which are not converted successfully by hipify, for instance:
thrust/system/cuda/detail/detail/launch_closure.inl:98:23.

[ToDo]
File a bug on cudaKernelCallExpr matcher for conversion error (thrust\examples\cuda\<any cu example>).


[ROCm/clr commit: afe6073d3f]
2017-02-14 16:28:05 +03:00
Evgeny Mankov 8c0f19aa7a [HIPIFY] Minor refactoring
+ insertHipHeaders function is added to Cuda2Hip class;
+ fix replacement ending for hip header.


[ROCm/clr commit: e5c601df45]
2017-02-13 18:13:49 +03:00
Maneesh Gupta c7b52142ae Generate package config for cmake
Change-Id: I73a0b21361bbe29e095dc515bdc70588ec722d57


[ROCm/clr commit: 57f7f4660a]
2017-02-13 16:01:50 +05:30
Paul 7476e0bfb5 Set hip version correctly
[ROCm/clr commit: f1f01ceb63]
2017-02-13 15:57:10 +05:30
Aditya Atluri 25210492b0 v3: added free for ihipModuleSymbol_t structures inside tracker
Change-Id: Ib8041a05312c08cbdf2d4fee5e7cbae17df6efff


[ROCm/clr commit: 1cffe49775]
2017-02-10 13:42:10 -06:00
Aditya Atluri 3577c19d66 v2: Fixed hipModule memory management
1. Changed test to assert for same hipFunction values
2. Added better memory management for hipModule

Change-Id: I10d7aef13c215a2211e262f3c79017f26a17d9a7


[ROCm/clr commit: 554fe191e1]
2017-02-10 13:32:13 -06:00
Evgeny Mankov 7ae02955f7 [HIPIFY] 'CHANGED LOC', 'TOTAL LOC' and 'CODE CHANGED (in lines)' are added to statistics.
[ROCm/clr commit: 25d4de9e95]
2017-02-10 22:02:41 +03:00
Maneesh Gupta ab2942538d Build libhip_hcc.so as a fat binary
Change-Id: Ie4f334d8f9576edf5df0f917f72083d7842eb193


[ROCm/clr commit: 3967ece8dd]
2017-02-10 10:32:04 +05:30
Aditya Atluri 5f8799a0a2 fixed shared memory usage implementation for hipDynamicShared2.cpp test
Change-Id: I34c72cb905f78de0f37e94174382e8be5c532028


[ROCm/clr commit: 307a21c946]
2017-02-09 18:17:42 -06:00
Aditya Atluri c5bcf5c096 added new dynamic shared mem test
Change-Id: Ic2a12fc9bc5b67e85f1e6c6008f10c7c66388377


[ROCm/clr commit: d6b5c02862]
2017-02-09 18:07:48 -06:00
Aditya Atluri 6c76483ac8 fixed hipFunction memory management
Change-Id: I7ebb323419bcd220ebd6466a8eb38e7bfdb1520a


[ROCm/clr commit: 6110fcdfb6]
2017-02-09 17:22:55 -06:00
Maneesh Gupta 7a146c9d3d Update hip_hcc packaging script
Change-Id: I2dc96545c472942bcf2bc8a2e88735f3ba26d1e1


[ROCm/clr commit: 7f62529b1f]
2017-02-09 20:28:28 +05:30
Maneesh Gupta 90a03f8684 Disable failing directed tests
- hipTestDeviceSymbol
- hipTestConstant
- hipTestMallocKernel

Change-Id: Ibfe9fc0b8a59882f1de64b42e18777a7bd56ee97


[ROCm/clr commit: 6659eb8d16]
2017-02-09 14:48:22 +05:30
Maneesh Gupta 2b6171816d Fix arch specific hcc extra libs env var
Change-Id: I7429da2f1cb98750d6a9601e7e5bde844a098487


[ROCm/clr commit: 71363810dd]
2017-02-09 14:38:39 +05:30
Aditya Atluri ba45e02007 added architecture specific macros
1. Added __HIP_ARCH_GFXNUM__
2. Usage, -D__HIP_ARCH_GFX803__=1

Change-Id: I68b3a85d62cfab3a45d2b7a70cb3518ab2565236


[ROCm/clr commit: c6c90f6f5a]
2017-02-08 19:45:32 -06:00
pensun b411549397 Add pseudo code example for hip_bugs.md
Change-Id: Ia2af8e6165faeb3fbb81428e20d4dc5b19b2fa9e


[ROCm/clr commit: f2bfc8a405]
2017-02-08 16:20:01 -06:00
Aditya Atluri 76a58521f5 fixed hipcc for new compiler flags
Change-Id: I49ec059be20ff26b7482c84d91ab7a43826c6a8d


[ROCm/clr commit: 400d0d4f78]
2017-02-08 14:06:01 -06:00
Aditya Atluri 248b42d3e3 include arch specific ir on fallback path
Change-Id: Ib04996aae2c21eb73ef2a9f6305915e0caccd704


[ROCm/clr commit: 26b5e57cfd]
2017-02-08 12:19:06 -06:00
Aditya Atluri 14dcdff8f4 Fixed Hawaii link issues
1. Split hip_ir.ll to hip_hc.ll and hip_hc_gfx803.ll
 a. hip_hc.ll contains arch generic ir implementations
 b. hip_hc_gfx803.ll contains gfx803 (fiji, polaris) specific ir
2. HIPCC can now parse --amdgpu-target=*.
 a. Usage: hipcc --amdgpu-target=gfx803 --amdgpu-target=gfx701
 b. TODO: Convert to --amdgpu-target=gfx803,gfx701
3. With LLC in HCC able to generate native f16 isa, removed inline half asm math ops
4. Fixed threadfence and threadfence_block to use functions in rocdl

Change-Id: Ic9a9e3e04139b0d75d2c2a263c030ca77adc1019


[ROCm/clr commit: 60ec83c683]
2017-02-08 12:04:05 -06:00
Evgeny Mankov 2cef50ac30 [HIPIFY] Readme.md update.
[ROCm/clr commit: cc8a7f3d3e]
2017-02-08 19:50:05 +03:00