BareMetal.cpp 12 KB

123456789101112131415161718192021222324252627282930313233343536373839404142434445464748495051525354555657585960616263646566676869707172737475767778798081828384858687888990919293949596979899100101102103104105106107108109110111112113114115116117118119120121122123124125126127128129130131132133134135136137138139140141142143144145146147148149150151152153154155156157158159160161162163164165166167168169170171172173174175176177178179180181182183184185186187188189190191192193194195196197198199200201202203204205206207208209210211212213214215216217218219220221222223224225226227228229230231232233234235236237238239240241242243244245246247248249250251252253254255256257258259260261262263264265266267268269270271272273274275276277278279280281282283284285286287288289290291292293294295296297298299300301302303304305306307308309310311312313314315316317318319320321322323324325326327328329330331332333334335336337338339340341342343344345346
  1. //===-- BareMetal.cpp - Bare Metal ToolChain --------------------*- 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 "BareMetal.h"
  9. #include "CommonArgs.h"
  10. #include "Gnu.h"
  11. #include "clang/Driver/InputInfo.h"
  12. #include "Arch/RISCV.h"
  13. #include "clang/Driver/Compilation.h"
  14. #include "clang/Driver/Driver.h"
  15. #include "clang/Driver/DriverDiagnostic.h"
  16. #include "clang/Driver/Options.h"
  17. #include "llvm/Option/ArgList.h"
  18. #include "llvm/Support/Path.h"
  19. #include "llvm/Support/VirtualFileSystem.h"
  20. #include "llvm/Support/raw_ostream.h"
  21. using namespace llvm::opt;
  22. using namespace clang;
  23. using namespace clang::driver;
  24. using namespace clang::driver::tools;
  25. using namespace clang::driver::toolchains;
  26. static Multilib makeMultilib(StringRef commonSuffix) {
  27. return Multilib(commonSuffix, commonSuffix, commonSuffix);
  28. }
  29. static bool findRISCVMultilibs(const Driver &D,
  30. const llvm::Triple &TargetTriple,
  31. const ArgList &Args, DetectedMultilibs &Result) {
  32. Multilib::flags_list Flags;
  33. StringRef Arch = riscv::getRISCVArch(Args, TargetTriple);
  34. StringRef Abi = tools::riscv::getRISCVABI(Args, TargetTriple);
  35. if (TargetTriple.isRISCV64()) {
  36. Multilib Imac = makeMultilib("").flag("+march=rv64imac").flag("+mabi=lp64");
  37. Multilib Imafdc = makeMultilib("/rv64imafdc/lp64d")
  38. .flag("+march=rv64imafdc")
  39. .flag("+mabi=lp64d");
  40. // Multilib reuse
  41. bool UseImafdc =
  42. (Arch == "rv64imafdc") || (Arch == "rv64gc"); // gc => imafdc
  43. addMultilibFlag((Arch == "rv64imac"), "march=rv64imac", Flags);
  44. addMultilibFlag(UseImafdc, "march=rv64imafdc", Flags);
  45. addMultilibFlag(Abi == "lp64", "mabi=lp64", Flags);
  46. addMultilibFlag(Abi == "lp64d", "mabi=lp64d", Flags);
  47. Result.Multilibs = MultilibSet().Either(Imac, Imafdc);
  48. return Result.Multilibs.select(Flags, Result.SelectedMultilib);
  49. }
  50. if (TargetTriple.isRISCV32()) {
  51. Multilib Imac =
  52. makeMultilib("").flag("+march=rv32imac").flag("+mabi=ilp32");
  53. Multilib I =
  54. makeMultilib("/rv32i/ilp32").flag("+march=rv32i").flag("+mabi=ilp32");
  55. Multilib Im =
  56. makeMultilib("/rv32im/ilp32").flag("+march=rv32im").flag("+mabi=ilp32");
  57. Multilib Iac = makeMultilib("/rv32iac/ilp32")
  58. .flag("+march=rv32iac")
  59. .flag("+mabi=ilp32");
  60. Multilib Imafc = makeMultilib("/rv32imafc/ilp32f")
  61. .flag("+march=rv32imafc")
  62. .flag("+mabi=ilp32f");
  63. // Multilib reuse
  64. bool UseI = (Arch == "rv32i") || (Arch == "rv32ic"); // ic => i
  65. bool UseIm = (Arch == "rv32im") || (Arch == "rv32imc"); // imc => im
  66. bool UseImafc = (Arch == "rv32imafc") || (Arch == "rv32imafdc") ||
  67. (Arch == "rv32gc"); // imafdc,gc => imafc
  68. addMultilibFlag(UseI, "march=rv32i", Flags);
  69. addMultilibFlag(UseIm, "march=rv32im", Flags);
  70. addMultilibFlag((Arch == "rv32iac"), "march=rv32iac", Flags);
  71. addMultilibFlag((Arch == "rv32imac"), "march=rv32imac", Flags);
  72. addMultilibFlag(UseImafc, "march=rv32imafc", Flags);
  73. addMultilibFlag(Abi == "ilp32", "mabi=ilp32", Flags);
  74. addMultilibFlag(Abi == "ilp32f", "mabi=ilp32f", Flags);
  75. Result.Multilibs = MultilibSet().Either(I, Im, Iac, Imac, Imafc);
  76. return Result.Multilibs.select(Flags, Result.SelectedMultilib);
  77. }
  78. return false;
  79. }
  80. BareMetal::BareMetal(const Driver &D, const llvm::Triple &Triple,
  81. const ArgList &Args)
  82. : ToolChain(D, Triple, Args) {
  83. getProgramPaths().push_back(getDriver().getInstalledDir());
  84. if (getDriver().getInstalledDir() != getDriver().Dir)
  85. getProgramPaths().push_back(getDriver().Dir);
  86. findMultilibs(D, Triple, Args);
  87. SmallString<128> SysRoot(computeSysRoot());
  88. if (!SysRoot.empty()) {
  89. llvm::sys::path::append(SysRoot, "lib");
  90. getFilePaths().push_back(std::string(SysRoot));
  91. getLibraryPaths().push_back(std::string(SysRoot));
  92. }
  93. }
  94. /// Is the triple {arm,thumb}-none-none-{eabi,eabihf} ?
  95. static bool isARMBareMetal(const llvm::Triple &Triple) {
  96. if (Triple.getArch() != llvm::Triple::arm &&
  97. Triple.getArch() != llvm::Triple::thumb)
  98. return false;
  99. if (Triple.getVendor() != llvm::Triple::UnknownVendor)
  100. return false;
  101. if (Triple.getOS() != llvm::Triple::UnknownOS)
  102. return false;
  103. if (Triple.getEnvironment() != llvm::Triple::EABI &&
  104. Triple.getEnvironment() != llvm::Triple::EABIHF)
  105. return false;
  106. return true;
  107. }
  108. /// Is the triple aarch64-none-elf?
  109. static bool isAArch64BareMetal(const llvm::Triple &Triple) {
  110. if (Triple.getArch() != llvm::Triple::aarch64)
  111. return false;
  112. if (Triple.getVendor() != llvm::Triple::UnknownVendor)
  113. return false;
  114. if (Triple.getOS() != llvm::Triple::UnknownOS)
  115. return false;
  116. return Triple.getEnvironmentName() == "elf";
  117. }
  118. static bool isRISCVBareMetal(const llvm::Triple &Triple) {
  119. if (!Triple.isRISCV())
  120. return false;
  121. if (Triple.getVendor() != llvm::Triple::UnknownVendor)
  122. return false;
  123. if (Triple.getOS() != llvm::Triple::UnknownOS)
  124. return false;
  125. return Triple.getEnvironmentName() == "elf";
  126. }
  127. void BareMetal::findMultilibs(const Driver &D, const llvm::Triple &Triple,
  128. const ArgList &Args) {
  129. DetectedMultilibs Result;
  130. if (isRISCVBareMetal(Triple)) {
  131. if (findRISCVMultilibs(D, Triple, Args, Result)) {
  132. SelectedMultilib = Result.SelectedMultilib;
  133. Multilibs = Result.Multilibs;
  134. }
  135. }
  136. }
  137. bool BareMetal::handlesTarget(const llvm::Triple &Triple) {
  138. return isARMBareMetal(Triple) || isAArch64BareMetal(Triple) ||
  139. isRISCVBareMetal(Triple);
  140. }
  141. Tool *BareMetal::buildLinker() const {
  142. return new tools::baremetal::Linker(*this);
  143. }
  144. std::string BareMetal::computeSysRoot() const {
  145. if (!getDriver().SysRoot.empty())
  146. return getDriver().SysRoot + SelectedMultilib.osSuffix();
  147. SmallString<128> SysRootDir;
  148. llvm::sys::path::append(SysRootDir, getDriver().Dir, "../lib/clang-runtimes",
  149. getDriver().getTargetTriple());
  150. SysRootDir += SelectedMultilib.osSuffix();
  151. return std::string(SysRootDir);
  152. }
  153. void BareMetal::AddClangSystemIncludeArgs(const ArgList &DriverArgs,
  154. ArgStringList &CC1Args) const {
  155. if (DriverArgs.hasArg(options::OPT_nostdinc))
  156. return;
  157. if (!DriverArgs.hasArg(options::OPT_nobuiltininc)) {
  158. SmallString<128> Dir(getDriver().ResourceDir);
  159. llvm::sys::path::append(Dir, "include");
  160. addSystemInclude(DriverArgs, CC1Args, Dir.str());
  161. }
  162. if (!DriverArgs.hasArg(options::OPT_nostdlibinc)) {
  163. SmallString<128> Dir(computeSysRoot());
  164. if (!Dir.empty()) {
  165. llvm::sys::path::append(Dir, "include");
  166. addSystemInclude(DriverArgs, CC1Args, Dir.str());
  167. }
  168. }
  169. }
  170. void BareMetal::addClangTargetOptions(const ArgList &DriverArgs,
  171. ArgStringList &CC1Args,
  172. Action::OffloadKind) const {
  173. CC1Args.push_back("-nostdsysteminc");
  174. }
  175. void BareMetal::AddClangCXXStdlibIncludeArgs(const ArgList &DriverArgs,
  176. ArgStringList &CC1Args) const {
  177. if (DriverArgs.hasArg(options::OPT_nostdinc) ||
  178. DriverArgs.hasArg(options::OPT_nostdlibinc) ||
  179. DriverArgs.hasArg(options::OPT_nostdincxx))
  180. return;
  181. const Driver &D = getDriver();
  182. std::string SysRoot(computeSysRoot());
  183. if (SysRoot.empty())
  184. return;
  185. switch (GetCXXStdlibType(DriverArgs)) {
  186. case ToolChain::CST_Libcxx: {
  187. // First check sysroot/usr/include/c++/v1 if it exists.
  188. SmallString<128> TargetDir(SysRoot);
  189. llvm::sys::path::append(TargetDir, "usr", "include", "c++", "v1");
  190. if (D.getVFS().exists(TargetDir)) {
  191. addSystemInclude(DriverArgs, CC1Args, TargetDir.str());
  192. break;
  193. }
  194. // Add generic path if nothing else succeeded so far.
  195. SmallString<128> Dir(SysRoot);
  196. llvm::sys::path::append(Dir, "include", "c++", "v1");
  197. addSystemInclude(DriverArgs, CC1Args, Dir.str());
  198. break;
  199. }
  200. case ToolChain::CST_Libstdcxx: {
  201. SmallString<128> Dir(SysRoot);
  202. llvm::sys::path::append(Dir, "include", "c++");
  203. std::error_code EC;
  204. Generic_GCC::GCCVersion Version = {"", -1, -1, -1, "", "", ""};
  205. // Walk the subdirs, and find the one with the newest gcc version:
  206. for (llvm::vfs::directory_iterator LI = D.getVFS().dir_begin(Dir.str(), EC),
  207. LE;
  208. !EC && LI != LE; LI = LI.increment(EC)) {
  209. StringRef VersionText = llvm::sys::path::filename(LI->path());
  210. auto CandidateVersion = Generic_GCC::GCCVersion::Parse(VersionText);
  211. if (CandidateVersion.Major == -1)
  212. continue;
  213. if (CandidateVersion <= Version)
  214. continue;
  215. Version = CandidateVersion;
  216. }
  217. if (Version.Major == -1)
  218. return;
  219. llvm::sys::path::append(Dir, Version.Text);
  220. addSystemInclude(DriverArgs, CC1Args, Dir.str());
  221. break;
  222. }
  223. }
  224. }
  225. void BareMetal::AddCXXStdlibLibArgs(const ArgList &Args,
  226. ArgStringList &CmdArgs) const {
  227. switch (GetCXXStdlibType(Args)) {
  228. case ToolChain::CST_Libcxx:
  229. CmdArgs.push_back("-lc++");
  230. if (Args.hasArg(options::OPT_fexperimental_library))
  231. CmdArgs.push_back("-lc++experimental");
  232. CmdArgs.push_back("-lc++abi");
  233. break;
  234. case ToolChain::CST_Libstdcxx:
  235. CmdArgs.push_back("-lstdc++");
  236. CmdArgs.push_back("-lsupc++");
  237. break;
  238. }
  239. CmdArgs.push_back("-lunwind");
  240. }
  241. void BareMetal::AddLinkRuntimeLib(const ArgList &Args,
  242. ArgStringList &CmdArgs) const {
  243. ToolChain::RuntimeLibType RLT = GetRuntimeLibType(Args);
  244. switch (RLT) {
  245. case ToolChain::RLT_CompilerRT: {
  246. const std::string FileName = getCompilerRT(Args, "builtins");
  247. llvm::StringRef BaseName = llvm::sys::path::filename(FileName);
  248. BaseName.consume_front("lib");
  249. BaseName.consume_back(".a");
  250. CmdArgs.push_back(Args.MakeArgString("-l" + BaseName));
  251. return;
  252. }
  253. case ToolChain::RLT_Libgcc:
  254. CmdArgs.push_back("-lgcc");
  255. return;
  256. }
  257. llvm_unreachable("Unhandled RuntimeLibType.");
  258. }
  259. void baremetal::Linker::ConstructJob(Compilation &C, const JobAction &JA,
  260. const InputInfo &Output,
  261. const InputInfoList &Inputs,
  262. const ArgList &Args,
  263. const char *LinkingOutput) const {
  264. ArgStringList CmdArgs;
  265. auto &TC = static_cast<const toolchains::BareMetal &>(getToolChain());
  266. AddLinkerInputs(TC, Inputs, Args, CmdArgs, JA);
  267. CmdArgs.push_back("-Bstatic");
  268. Args.AddAllArgs(CmdArgs, {options::OPT_L, options::OPT_T_Group,
  269. options::OPT_e, options::OPT_s, options::OPT_t,
  270. options::OPT_Z_Flag, options::OPT_r});
  271. TC.AddFilePathLibArgs(Args, CmdArgs);
  272. for (const auto &LibPath : TC.getLibraryPaths())
  273. CmdArgs.push_back(Args.MakeArgString(llvm::Twine("-L", LibPath)));
  274. const std::string FileName = TC.getCompilerRT(Args, "builtins");
  275. llvm::SmallString<128> PathBuf{FileName};
  276. llvm::sys::path::remove_filename(PathBuf);
  277. CmdArgs.push_back(Args.MakeArgString("-L" + PathBuf));
  278. if (TC.ShouldLinkCXXStdlib(Args))
  279. TC.AddCXXStdlibLibArgs(Args, CmdArgs);
  280. if (!Args.hasArg(options::OPT_nostdlib, options::OPT_nodefaultlibs)) {
  281. CmdArgs.push_back("-lc");
  282. CmdArgs.push_back("-lm");
  283. TC.AddLinkRuntimeLib(Args, CmdArgs);
  284. }
  285. CmdArgs.push_back("-o");
  286. CmdArgs.push_back(Output.getFilename());
  287. C.addCommand(std::make_unique<Command>(JA, *this, ResponseFileSupport::None(),
  288. Args.MakeArgString(TC.GetLinkerPath()),
  289. CmdArgs, Inputs, Output));
  290. }