1 //===--- BaremMetal.cpp - Bare Metal ToolChain ------------------*- C++ -*-===//
3 // The LLVM Compiler Infrastructure
5 // This file is distributed under the University of Illinois Open Source
6 // License. See LICENSE.TXT for details.
8 //===----------------------------------------------------------------------===//
10 #include "BareMetal.h"
12 #include "CommonArgs.h"
13 #include "InputInfo.h"
16 #include "clang/Basic/VirtualFileSystem.h"
17 #include "clang/Driver/Compilation.h"
18 #include "clang/Driver/Driver.h"
19 #include "clang/Driver/DriverDiagnostic.h"
20 #include "clang/Driver/Options.h"
21 #include "llvm/Option/ArgList.h"
22 #include "llvm/Support/Path.h"
23 #include "llvm/Support/raw_ostream.h"
25 using namespace llvm::opt;
26 using namespace clang;
27 using namespace clang::driver;
28 using namespace clang::driver::tools;
29 using namespace clang::driver::toolchains;
31 BareMetal::BareMetal(const Driver &D, const llvm::Triple &Triple,
33 : ToolChain(D, Triple, Args) {
34 getProgramPaths().push_back(getDriver().getInstalledDir());
35 if (getDriver().getInstalledDir() != getDriver().Dir)
36 getProgramPaths().push_back(getDriver().Dir);
39 BareMetal::~BareMetal() {}
41 /// Is the triple {arm,thumb}-none-none-{eabi,eabihf} ?
42 static bool isARMBareMetal(const llvm::Triple &Triple) {
43 if (Triple.getArch() != llvm::Triple::arm &&
44 Triple.getArch() != llvm::Triple::thumb)
47 if (Triple.getVendor() != llvm::Triple::UnknownVendor)
50 if (Triple.getOS() != llvm::Triple::UnknownOS)
53 if (Triple.getEnvironment() != llvm::Triple::EABI &&
54 Triple.getEnvironment() != llvm::Triple::EABIHF)
60 bool BareMetal::handlesTarget(const llvm::Triple &Triple) {
61 return isARMBareMetal(Triple);
64 Tool *BareMetal::buildLinker() const {
65 return new tools::baremetal::Linker(*this);
68 std::string BareMetal::getThreadModel() const {
72 bool BareMetal::isThreadModelSupported(const StringRef Model) const {
73 return Model == "single";
76 std::string BareMetal::getRuntimesDir() const {
77 SmallString<128> Dir(getDriver().ResourceDir);
78 llvm::sys::path::append(Dir, "lib", "baremetal");
82 void BareMetal::AddClangSystemIncludeArgs(const ArgList &DriverArgs,
83 ArgStringList &CC1Args) const {
84 if (DriverArgs.hasArg(options::OPT_nostdinc))
87 if (!DriverArgs.hasArg(options::OPT_nobuiltininc)) {
88 SmallString<128> Dir(getDriver().ResourceDir);
89 llvm::sys::path::append(Dir, "include");
90 addSystemInclude(DriverArgs, CC1Args, Dir.str());
93 if (!DriverArgs.hasArg(options::OPT_nostdlibinc)) {
94 SmallString<128> Dir(getDriver().SysRoot);
95 llvm::sys::path::append(Dir, "include");
96 addSystemInclude(DriverArgs, CC1Args, Dir.str());
100 void BareMetal::addClangTargetOptions(const ArgList &DriverArgs,
101 ArgStringList &CC1Args,
102 Action::OffloadKind) const {
103 CC1Args.push_back("-nostdsysteminc");
106 std::string BareMetal::findLibCxxIncludePath(CXXStdlibType LibType) const {
107 StringRef SysRoot = getDriver().SysRoot;
112 case ToolChain::CST_Libcxx: {
113 SmallString<128> Dir(SysRoot);
114 llvm::sys::path::append(Dir, "include", "c++", "v1");
117 case ToolChain::CST_Libstdcxx: {
118 SmallString<128> Dir(SysRoot);
119 llvm::sys::path::append(Dir, "include", "c++");
121 Generic_GCC::GCCVersion Version = {"", -1, -1, -1, "", "", ""};
122 // Walk the subdirs, and find the one with the newest gcc version:
123 for (vfs::directory_iterator LI =
124 getDriver().getVFS().dir_begin(Dir.str(), EC), LE;
125 !EC && LI != LE; LI = LI.increment(EC)) {
126 StringRef VersionText = llvm::sys::path::filename(LI->getName());
127 auto CandidateVersion = Generic_GCC::GCCVersion::Parse(VersionText);
128 if (CandidateVersion.Major == -1)
130 if (CandidateVersion <= Version)
132 Version = CandidateVersion;
134 if (Version.Major == -1)
136 llvm::sys::path::append(Dir, Version.Text);
140 llvm_unreachable("unhandled LibType");
143 void BareMetal::AddClangCXXStdlibIncludeArgs(
144 const ArgList &DriverArgs, ArgStringList &CC1Args) const {
145 if (DriverArgs.hasArg(options::OPT_nostdinc) ||
146 DriverArgs.hasArg(options::OPT_nostdlibinc) ||
147 DriverArgs.hasArg(options::OPT_nostdincxx))
150 std::string Path = findLibCxxIncludePath(GetCXXStdlibType(DriverArgs));
152 addSystemInclude(DriverArgs, CC1Args, Path);
155 void BareMetal::AddCXXStdlibLibArgs(const ArgList &Args,
156 ArgStringList &CmdArgs) const {
157 switch (GetCXXStdlibType(Args)) {
158 case ToolChain::CST_Libcxx:
159 CmdArgs.push_back("-lc++");
160 CmdArgs.push_back("-lc++abi");
162 case ToolChain::CST_Libstdcxx:
163 CmdArgs.push_back("-lstdc++");
164 CmdArgs.push_back("-lsupc++");
167 CmdArgs.push_back("-lunwind");
170 void BareMetal::AddLinkRuntimeLib(const ArgList &Args,
171 ArgStringList &CmdArgs) const {
172 CmdArgs.push_back(Args.MakeArgString("-lclang_rt.builtins-" +
173 getTriple().getArchName() + ".a"));
176 void baremetal::Linker::ConstructJob(Compilation &C, const JobAction &JA,
177 const InputInfo &Output,
178 const InputInfoList &Inputs,
180 const char *LinkingOutput) const {
181 ArgStringList CmdArgs;
183 auto &TC = static_cast<const toolchains::BareMetal&>(getToolChain());
185 AddLinkerInputs(TC, Inputs, Args, CmdArgs, JA);
187 CmdArgs.push_back("-Bstatic");
189 CmdArgs.push_back(Args.MakeArgString("-L" + TC.getRuntimesDir()));
191 Args.AddAllArgs(CmdArgs, {options::OPT_L, options::OPT_T_Group,
192 options::OPT_e, options::OPT_s, options::OPT_t,
193 options::OPT_Z_Flag, options::OPT_r});
195 if (!Args.hasArg(options::OPT_nostdlib, options::OPT_nodefaultlibs)) {
196 if (C.getDriver().CCCIsCXX())
197 TC.AddCXXStdlibLibArgs(Args, CmdArgs);
199 CmdArgs.push_back("-lc");
200 CmdArgs.push_back("-lm");
202 TC.AddLinkRuntimeLib(Args, CmdArgs);
205 CmdArgs.push_back("-o");
206 CmdArgs.push_back(Output.getFilename());
208 C.addCommand(llvm::make_unique<Command>(JA, *this,
209 Args.MakeArgString(TC.GetLinkerPath()),