Skip to content

Conversation

atamazov
Copy link
Contributor

@atamazov atamazov commented Nov 26, 2020

Resolves issues related to SWDEV-257056:

  • Fixed: Observed MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in handle_test.
  • Fixed: Observed MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in reduction_operator.hpp (fixes reduce_test).
  • Fixed: Observed MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in ConvAsmImplicitGemmV4R1DynamicWrw.
  • Fixed: handle_test for the case when HIP kernels disabled.
  • Fixed: Incorrect #include in kernel source.
  • Added: Workaround in handle_test for macros missing from HIP PCH in ROCm, 3.10 RC3
    • Macro: WORKAROUND_SWDEV_257056_PCH_MISSING_MACROS.
    • The workaround is enabled by default.
    • It will be disabled automatically as soon as ROCm version exceeds 3.10.x
  • Added feature: Introduced env var control MIOPEN_DEBUG_COMGR_HIP_PCH_ENFORCE that allows overriding of HIP PCH feature auto-detection.
  • Added: Workaround for incorrectly reported support for HIP PCH in ROCm 3.9

@daniellowell
Copy link

@fronteer @shaojiewang @JehandadKhan You are all assigned to review this urgent PR, please do so.

return HIP_SUPPORTS_PCH;
}

static std::string GetPchEnableStatus()

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

I feel like this could be useful elsewhere and not just logging.

Copy link
Contributor Author

@atamazov atamazov Dec 1, 2020

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

Only here so far. Any ideas?

@codecov
Copy link

codecov bot commented Dec 2, 2020

Codecov Report

Merging #627 (09b47de) into develop (939ced1) will decrease coverage by 0.91%.
The diff coverage is 80.00%.

Impacted file tree graph

@@             Coverage Diff             @@
##           develop     #627      +/-   ##
===========================================
- Coverage    53.02%   52.11%   -0.92%     
===========================================
  Files          297      297              
  Lines        45814    45814              
===========================================
- Hits         24294    23877     -417     
- Misses       21520    21937     +417     
Impacted Files Coverage Δ
src/include/miopen/execution_context.hpp 70.00% <ø> (ø)
test/handle_test.cpp 77.94% <75.00%> (ø)
src/execution_context.cpp 81.92% <100.00%> (ø)
src/solver/conv_hip_implicit_gemm_v4r4.cpp 6.31% <0.00%> (-64.08%) ⬇️
src/invoker_cache.cpp 81.81% <0.00%> (-4.55%) ⬇️
src/conv/invokers/impl_gemm_dynamic.cpp 93.83% <0.00%> (-3.97%) ⬇️
src/gemm_v2.cpp 56.37% <0.00%> (-3.46%) ⬇️
src/solver/conv_asm_5x10u2v2b1.cpp 31.25% <0.00%> (-3.13%) ⬇️
src/include/miopen/solver.hpp 15.04% <0.00%> (-2.95%) ⬇️
src/md5.cpp 90.57% <0.00%> (-2.90%) ⬇️
... and 24 more

Continue to review full report at Codecov.

Legend - Click here to learn more
Δ = absolute <relative> (impact), ø = not affected, ? = missing data
Powered by Codecov. Last update 1aee58f...09b47de. Read the comment docs.

JehandadKhan
JehandadKhan previously approved these changes Dec 2, 2020
@atamazov
Copy link
Contributor Author

atamazov commented Dec 2, 2020

Description updated.

@daniellowell daniellowell self-requested a review December 5, 2020 15:56
@daniellowell daniellowell merged commit c8a7416 into develop Dec 5, 2020
jeffdaily pushed a commit to jeffdaily/MIOpen that referenced this pull request Jan 6, 2021
* comgr-hip-pch-fix(01) Observe MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in handle_test
* comgr-hip-pch-fix(02) Observe MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in ConvAsmImplicitGemmV4R1DynamicWrw
* comgr-hip-pch-fix(03) Observe MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in handle_test (leftovers)
* comgr-hip-pch-fix(04) Add MIOPEN_DEBUG_COMGR_HIP_PCH_DISABLE
* comgr-hip-pch-fix(05) Allow forced enabled & disabled PCH. MIOPEN_DEBUG_COMGR_HIP_PCH_DISABLE -> ...ENFORCE
* comgr-hip-pch-fix(06) Observe MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in reduction_operator.hpp (fixes reduce_test)
* comgr-hip-pch-fix(07) Fix incorrect #include in kernel source
* comgr-hip-pch-fix(08) Temporary W/A for handle_test
* comgr-hip-pch-fix(09) Disable W/A for handle_test
* comgr-hip-pch-fix(10) handle_test: Fix for the case when HIP kernels disabled. Rename W/A macro.
* comgr-hip-pch-fix(11) Automatically disable W/A in handle test after ROCm 3.10
* comgr-hip-pch-fix(13) W/A: Disable HIP PCH for ROCm <= 3.9.x
daniellowell pushed a commit that referenced this pull request Jan 8, 2021
* comgr-hip-pch-fix(01) Observe MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in handle_test
* comgr-hip-pch-fix(02) Observe MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in ConvAsmImplicitGemmV4R1DynamicWrw
* comgr-hip-pch-fix(03) Observe MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in handle_test (leftovers)
* comgr-hip-pch-fix(04) Add MIOPEN_DEBUG_COMGR_HIP_PCH_DISABLE
* comgr-hip-pch-fix(05) Allow forced enabled & disabled PCH. MIOPEN_DEBUG_COMGR_HIP_PCH_DISABLE -> ...ENFORCE
* comgr-hip-pch-fix(06) Observe MIOPEN_DONT_USE_HIP_RUNTIME_HEADERS in reduction_operator.hpp (fixes reduce_test)
* comgr-hip-pch-fix(07) Fix incorrect #include in kernel source
* comgr-hip-pch-fix(08) Temporary W/A for handle_test
* comgr-hip-pch-fix(09) Disable W/A for handle_test
* comgr-hip-pch-fix(10) handle_test: Fix for the case when HIP kernels disabled. Rename W/A macro.
* comgr-hip-pch-fix(11) Automatically disable W/A in handle test after ROCm 3.10
* comgr-hip-pch-fix(13) W/A: Disable HIP PCH for ROCm <= 3.9.x
@atamazov atamazov deleted the comgr-hip-pch-fix branch January 21, 2021 22:37
@atamazov atamazov mentioned this pull request Mar 26, 2023
Sign up for free to join this conversation on GitHub. Already have an account? Sign in to comment
Projects
None yet
Development

Successfully merging this pull request may close these issues.

[Comgr] Unknown type name occurred while compiling kernel
3 participants