clang 22.0.0git
SPIRV.cpp
Go to the documentation of this file.
1//===--- SPIRV.cpp - SPIR-V Tool Implementations ----------------*- C++ -*-===//
2//
3// Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
4// See https://llvm.org/LICENSE.txt for license information.
5// SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
6//
7//===----------------------------------------------------------------------===//
8#include "SPIRV.h"
11#include "clang/Driver/Driver.h"
14
15using namespace clang::driver;
16using namespace clang::driver::toolchains;
17using namespace clang::driver::tools;
18using namespace llvm::opt;
19
21 const JobAction &JA,
22 const InputInfo &Output,
23 const InputInfo &Input,
24 const llvm::opt::ArgStringList &Args) {
25 llvm::opt::ArgStringList CmdArgs(Args);
26 CmdArgs.push_back(Input.getFilename());
27
28 assert(Input.getType() != types::TY_PP_Asm && "Unexpected input type");
29
30 if (Output.getType() == types::TY_PP_Asm)
31 CmdArgs.push_back("--spirv-tools-dis");
32
33 CmdArgs.append({"-o", Output.getFilename()});
34
35 // Try to find "llvm-spirv-<LLVM_VERSION_MAJOR>". Otherwise, fall back to
36 // plain "llvm-spirv".
37 using namespace std::string_literals;
38 auto VersionedTool = "llvm-spirv-"s + std::to_string(LLVM_VERSION_MAJOR);
39 std::string ExeCand = T.getToolChain().GetProgramPath(VersionedTool.c_str());
40 if (!llvm::sys::fs::can_execute(ExeCand))
41 ExeCand = T.getToolChain().GetProgramPath("llvm-spirv");
42
43 const char *Exec = C.getArgs().MakeArgString(ExeCand);
44 C.addCommand(std::make_unique<Command>(JA, T, ResponseFileSupport::None(),
45 Exec, CmdArgs, Input, Output));
46}
47
49 const JobAction &JA,
50 const InputInfo &Output,
51 const InputInfo &Input,
52 const llvm::opt::ArgStringList &Args) {
53 llvm::opt::ArgStringList CmdArgs(Args);
54 CmdArgs.push_back(Input.getFilename());
55
56 assert(Input.getType() == types::TY_PP_Asm && "Unexpected input type");
57
58 CmdArgs.append({"-o", Output.getFilename()});
59
60 // Try to find "spirv-as-<LLVM_VERSION_MAJOR>". Otherwise, fall back to
61 // plain "spirv-as".
62 using namespace std::string_literals;
63 auto VersionedTool = "spirv-as-"s + std::to_string(LLVM_VERSION_MAJOR);
64 std::string ExeCand = T.getToolChain().GetProgramPath(VersionedTool.c_str());
65 if (!llvm::sys::fs::can_execute(ExeCand))
66 ExeCand = T.getToolChain().GetProgramPath("spirv-as");
67
68 if (!llvm::sys::fs::can_execute(ExeCand) &&
69 !C.getArgs().hasArg(clang::options::OPT__HASH_HASH_HASH)) {
70 C.getDriver().Diag(clang::diag::err_drv_no_spv_tools) << "spirv-as";
71 return;
72 }
73 const char *Exec = C.getArgs().MakeArgString(ExeCand);
74 C.addCommand(std::make_unique<Command>(JA, T, ResponseFileSupport::None(),
75 Exec, CmdArgs, Input, Output));
76}
77
79 const InputInfo &Output,
80 const InputInfoList &Inputs,
81 const ArgList &Args,
82 const char *LinkingOutput) const {
83 claimNoWarnArgs(Args);
84 if (Inputs.size() != 1)
85 llvm_unreachable("Invalid number of input files.");
86 constructTranslateCommand(C, *this, JA, Output, Inputs[0], {});
87}
88
90 const InputInfo &Output,
91 const InputInfoList &Inputs,
92 const ArgList &Args,
93 const char *AssembleOutput) const {
94 claimNoWarnArgs(Args);
95 if (Inputs.size() != 1)
96 llvm_unreachable("Invalid number of input files.");
97 constructAssembleCommand(C, *this, JA, Output, Inputs[0], {});
98}
99
100clang::driver::Tool *SPIRVToolChain::getAssembler() const {
101 if (!Assembler)
102 Assembler = std::make_unique<SPIRV::Assembler>(*this);
103 return Assembler.get();
104}
105
110
112 switch (AC) {
113 default:
114 break;
116 return SPIRVToolChain::getAssembler();
117 }
118 return ToolChain::getTool(AC);
119}
123
125 const InputInfo &Output,
126 const InputInfoList &Inputs,
127 const ArgList &Args,
128 const char *LinkingOutput) const {
131 ArgStringList CmdArgs;
132 AddLinkerInputs(getToolChain(), Inputs, Args, CmdArgs, JA);
133
134 CmdArgs.push_back("-o");
135 CmdArgs.push_back(Output.getFilename());
136
137 // Use of --sycl-link will call the clang-sycl-linker instead of
138 // the default linker (spirv-link).
139 if (Args.hasArg(options::OPT_sycl_link))
140 Linker = ToolChain.GetProgramPath("clang-sycl-linker");
141 else if (!llvm::sys::fs::can_execute(Linker) &&
142 !C.getArgs().hasArg(clang::options::OPT__HASH_HASH_HASH)) {
143 C.getDriver().Diag(clang::diag::err_drv_no_spv_tools) << getShortName();
144 return;
145 }
146 C.addCommand(std::make_unique<Command>(JA, *this, ResponseFileSupport::None(),
147 Args.MakeArgString(Linker), CmdArgs,
148 Inputs, Output));
149}
150
151SPIRVToolChain::SPIRVToolChain(const Driver &D, const llvm::Triple &Triple,
152 const ArgList &Args)
153 : ToolChain(D, Triple, Args) {
154 // TODO: Revisit need/use of --sycl-link option once SYCL toolchain is
155 // available and SYCL linking support is moved there.
156 NativeLLVMSupport = Args.hasArg(options::OPT_sycl_link);
157}
158
159bool SPIRVToolChain::HasNativeLLVMSupport() const { return NativeLLVMSupport; }
__device__ __2f16 float __ockl_bool s
ActionClass getKind() const
Definition Action.h:149
Compilation - A set of tasks to perform for a single driver invocation.
Definition Compilation.h:45
Driver - Encapsulate logic for constructing compilation processes from a set of gcc-driver-like comma...
Definition Driver.h:99
InputInfo - Wrapper for information about an input source.
Definition InputInfo.h:22
const char * getFilename() const
Definition InputInfo.h:83
types::ID getType() const
Definition InputInfo.h:77
ToolChain - Access to tools for a single platform.
Definition ToolChain.h:92
ToolChain(const Driver &D, const llvm::Triple &T, const llvm::opt::ArgList &Args)
Definition ToolChain.cpp:89
std::string GetProgramPath(const char *Name) const
virtual Tool * getTool(Action::ActionClass AC) const
Tool - Information on a specific compilation tool.
Definition Tool.h:32
const ToolChain & getToolChain() const
Definition Tool.h:52
const char * getShortName() const
Definition Tool.h:50
Tool * buildLinker() const override
Definition SPIRV.cpp:120
clang::driver::Tool * getTool(Action::ActionClass AC) const override
Definition SPIRV.cpp:111
clang::driver::Tool * SelectTool(const JobAction &JA) const override
Choose a tool to use to handle the action JA.
Definition SPIRV.cpp:106
bool HasNativeLLVMSupport() const override
HasNativeLTOLinker - Check whether the linker and related tools have native LLVM support.
Definition SPIRV.cpp:159
SPIRVToolChain(const Driver &D, const llvm::Triple &Triple, const llvm::opt::ArgList &Args)
Definition SPIRV.cpp:151
void ConstructJob(Compilation &C, const JobAction &JA, const InputInfo &Output, const InputInfoList &Inputs, const llvm::opt::ArgList &TCArgs, const char *AssembleOutput) const override
ConstructJob - Construct jobs to perform the action JA, writing to Output and with Inputs,...
Definition SPIRV.cpp:89
Linker(const ToolChain &TC)
Definition SPIRV.h:46
void ConstructJob(Compilation &C, const JobAction &JA, const InputInfo &Output, const InputInfoList &Inputs, const llvm::opt::ArgList &TCArgs, const char *LinkingOutput) const override
ConstructJob - Construct jobs to perform the action JA, writing to Output and with Inputs,...
Definition SPIRV.cpp:124
void ConstructJob(Compilation &C, const JobAction &JA, const InputInfo &Output, const InputInfoList &Inputs, const llvm::opt::ArgList &TCArgs, const char *LinkingOutput) const override
ConstructJob - Construct jobs to perform the action JA, writing to Output and with Inputs,...
Definition SPIRV.cpp:78
void constructAssembleCommand(Compilation &C, const Tool &T, const JobAction &JA, const InputInfo &Output, const InputInfo &Input, const llvm::opt::ArgStringList &Args)
Definition SPIRV.cpp:48
void constructTranslateCommand(Compilation &C, const Tool &T, const JobAction &JA, const InputInfo &Output, const InputInfo &Input, const llvm::opt::ArgStringList &Args)
Definition SPIRV.cpp:20
void claimNoWarnArgs(const llvm::opt::ArgList &Args)
void AddLinkerInputs(const ToolChain &TC, const InputInfoList &Inputs, const llvm::opt::ArgList &Args, llvm::opt::ArgStringList &CmdArgs, const JobAction &JA)
SmallVector< InputInfo, 4 > InputInfoList
Definition Driver.h:50
const FunctionProtoType * T
static constexpr ResponseFileSupport None()
Returns a ResponseFileSupport indicating that response files are not supported.
Definition Job.h:78