File Manager

003 File Manager

Current Path: /usr/src/contrib/llvm-project/clang/lib/Driver/ToolChains

usr / src / contrib / llvm-project / clang / lib / Driver / ToolChains /

📁 ..
📄 AIX.cpp(7.69 KB)
📄 AIX.h(2.51 KB)
📄 AMDGPU.cpp(21.42 KB)
📄 AMDGPU.h(3.72 KB)
📄 AVR.cpp(5.72 KB)
📄 AVR.h(1.94 KB)
📄 Ananas.cpp(5.21 KB)
📄 Ananas.h(2.06 KB)
📁 Arch
📄 BareMetal.cpp(6.4 KB)
📄 BareMetal.h(2.96 KB)
📄 Clang.cpp(270.02 KB)
📄 Clang.h(7.82 KB)
📄 CloudABI.cpp(5.05 KB)
📄 CloudABI.h(2.3 KB)
📄 CommonArgs.cpp(49.63 KB)
📄 CommonArgs.h(5.95 KB)
📄 Contiki.cpp(926 B)
📄 Contiki.h(1.25 KB)
📄 CrossWindows.cpp(9.44 KB)
📄 CrossWindows.h(2.93 KB)
📄 Cuda.cpp(36.52 KB)
📄 Cuda.h(7.5 KB)
📄 Darwin.cpp(103.49 KB)
📄 Darwin.h(20.22 KB)
📄 DragonFly.cpp(6.83 KB)
📄 DragonFly.h(2.16 KB)
📄 Flang.cpp(2.57 KB)
📄 Flang.h(1.45 KB)
📄 FreeBSD.cpp(15.99 KB)
📄 FreeBSD.h(3.72 KB)
📄 Fuchsia.cpp(12.4 KB)
📄 Fuchsia.h(3.72 KB)
📄 Gnu.cpp(118.91 KB)
📄 Gnu.h(14.8 KB)
📄 HIP.cpp(15.47 KB)
📄 HIP.h(4.4 KB)
📄 Haiku.cpp(1.28 KB)
📄 Haiku.h(1.25 KB)
📄 Hexagon.cpp(23.79 KB)
📄 Hexagon.h(4.34 KB)
📄 Hurd.cpp(7.1 KB)
📄 Hurd.h(1.5 KB)
📄 InterfaceStubs.cpp(2.63 KB)
📄 InterfaceStubs.h(1.23 KB)
📄 Lanai.h(1.31 KB)
📄 Linux.cpp(32.88 KB)
📄 Linux.h(2.69 KB)
📄 MSP430.cpp(7.95 KB)
📄 MSP430.h(2.45 KB)
📄 MSVC.cpp(57.11 KB)
📄 MSVC.h(6.12 KB)
📄 MSVCSetupApi.h(19.2 KB)
📄 MinGW.cpp(21.52 KB)
📄 MinGW.h(3.8 KB)
📄 Minix.cpp(3.98 KB)
📄 Minix.h(2.05 KB)
📄 MipsLinux.cpp(4.48 KB)
📄 MipsLinux.h(1.98 KB)
📄 Myriad.cpp(11.75 KB)
📄 Myriad.h(3.73 KB)
📄 NaCl.cpp(13.25 KB)
📄 NaCl.h(3.01 KB)
📄 NetBSD.cpp(16.56 KB)
📄 NetBSD.h(2.97 KB)
📄 OpenBSD.cpp(10.17 KB)
📄 OpenBSD.h(3.31 KB)
📄 PPCLinux.cpp(1.06 KB)
📄 PPCLinux.h(1.05 KB)
📄 PS4CPU.cpp(9.53 KB)
📄 PS4CPU.h(3.68 KB)
📄 RISCVToolchain.cpp(7.25 KB)
📄 RISCVToolchain.h(2.28 KB)
📄 ROCm.h(6.94 KB)
📄 Solaris.cpp(10.41 KB)
📄 Solaris.h(2.5 KB)
📄 TCE.cpp(1.49 KB)
📄 TCE.h(1.49 KB)
📄 VEToolchain.cpp(4.09 KB)
📄 VEToolchain.h(2.16 KB)
📄 WebAssembly.cpp(13.53 KB)
📄 WebAssembly.h(2.94 KB)
📄 XCore.cpp(5.48 KB)
📄 XCore.h(2.98 KB)

Editing: BareMetal.cpp

//===-- BareMetal.cpp - Bare Metal ToolChain --------------------*- C++ -*-===//
//
// Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
// See https://llvm.org/LICENSE.txt for license information.
// SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
//
//===----------------------------------------------------------------------===//

#include "BareMetal.h"

#include "CommonArgs.h"
#include "InputInfo.h"
#include "Gnu.h"

#include "clang/Driver/Compilation.h"
#include "clang/Driver/Driver.h"
#include "clang/Driver/DriverDiagnostic.h"
#include "clang/Driver/Options.h"
#include "llvm/Option/ArgList.h"
#include "llvm/Support/Path.h"
#include "llvm/Support/VirtualFileSystem.h"
#include "llvm/Support/raw_ostream.h"

using namespace llvm::opt;
using namespace clang;
using namespace clang::driver;
using namespace clang::driver::tools;
using namespace clang::driver::toolchains;

BareMetal::BareMetal(const Driver &D, const llvm::Triple &Triple,
                           const ArgList &Args)
    : ToolChain(D, Triple, Args) {
  getProgramPaths().push_back(getDriver().getInstalledDir());
  if (getDriver().getInstalledDir() != getDriver().Dir)
    getProgramPaths().push_back(getDriver().Dir);
}

BareMetal::~BareMetal() {}

/// Is the triple {arm,thumb}-none-none-{eabi,eabihf} ?
static bool isARMBareMetal(const llvm::Triple &Triple) {
  if (Triple.getArch() != llvm::Triple::arm &&
      Triple.getArch() != llvm::Triple::thumb)
    return false;

if (Triple.getVendor() != llvm::Triple::UnknownVendor)
    return false;

if (Triple.getOS() != llvm::Triple::UnknownOS)
    return false;

if (Triple.getEnvironment() != llvm::Triple::EABI &&
      Triple.getEnvironment() != llvm::Triple::EABIHF)
    return false;

return true;
}

bool BareMetal::handlesTarget(const llvm::Triple &Triple) {
  return isARMBareMetal(Triple);
}

Tool *BareMetal::buildLinker() const {
  return new tools::baremetal::Linker(*this);
}

std::string BareMetal::getRuntimesDir() const {
  SmallString<128> Dir(getDriver().ResourceDir);
  llvm::sys::path::append(Dir, "lib", "baremetal");
  return std::string(Dir.str());
}

void BareMetal::AddClangSystemIncludeArgs(const ArgList &DriverArgs,
                                          ArgStringList &CC1Args) const {
  if (DriverArgs.hasArg(options::OPT_nostdinc))
    return;

if (!DriverArgs.hasArg(options::OPT_nobuiltininc)) {
    SmallString<128> Dir(getDriver().ResourceDir);
    llvm::sys::path::append(Dir, "include");
    addSystemInclude(DriverArgs, CC1Args, Dir.str());
  }

if (!DriverArgs.hasArg(options::OPT_nostdlibinc)) {
    SmallString<128> Dir(getDriver().SysRoot);
    llvm::sys::path::append(Dir, "include");
    addSystemInclude(DriverArgs, CC1Args, Dir.str());
  }
}

void BareMetal::addClangTargetOptions(const ArgList &DriverArgs,
                                      ArgStringList &CC1Args,
                                      Action::OffloadKind) const {
  CC1Args.push_back("-nostdsysteminc");
}

void BareMetal::AddClangCXXStdlibIncludeArgs(
    const ArgList &DriverArgs, ArgStringList &CC1Args) const {
  if (DriverArgs.hasArg(options::OPT_nostdinc) ||
      DriverArgs.hasArg(options::OPT_nostdlibinc) ||
      DriverArgs.hasArg(options::OPT_nostdincxx))
    return;

StringRef SysRoot = getDriver().SysRoot;
  if (SysRoot.empty())
    return;

switch (GetCXXStdlibType(DriverArgs)) {
  case ToolChain::CST_Libcxx: {
    SmallString<128> Dir(SysRoot);
    llvm::sys::path::append(Dir, "include", "c++", "v1");
    addSystemInclude(DriverArgs, CC1Args, Dir.str());
    break;
  }
  case ToolChain::CST_Libstdcxx: {
    SmallString<128> Dir(SysRoot);
    llvm::sys::path::append(Dir, "include", "c++");
    std::error_code EC;
    Generic_GCC::GCCVersion Version = {"", -1, -1, -1, "", "", ""};
    // Walk the subdirs, and find the one with the newest gcc version:
    for (llvm::vfs::directory_iterator
             LI = getDriver().getVFS().dir_begin(Dir.str(), EC),
             LE;
         !EC && LI != LE; LI = LI.increment(EC)) {
      StringRef VersionText = llvm::sys::path::filename(LI->path());
      auto CandidateVersion = Generic_GCC::GCCVersion::Parse(VersionText);
      if (CandidateVersion.Major == -1)
        continue;
      if (CandidateVersion <= Version)
        continue;
      Version = CandidateVersion;
    }
    if (Version.Major == -1)
      return;
    llvm::sys::path::append(Dir, Version.Text);
    addSystemInclude(DriverArgs, CC1Args, Dir.str());
    break;
  }
  }
}

void BareMetal::AddCXXStdlibLibArgs(const ArgList &Args,
                                    ArgStringList &CmdArgs) const {
  switch (GetCXXStdlibType(Args)) {
  case ToolChain::CST_Libcxx:
    CmdArgs.push_back("-lc++");
    CmdArgs.push_back("-lc++abi");
    break;
  case ToolChain::CST_Libstdcxx:
    CmdArgs.push_back("-lstdc++");
    CmdArgs.push_back("-lsupc++");
    break;
  }
  CmdArgs.push_back("-lunwind");
}

void BareMetal::AddLinkRuntimeLib(const ArgList &Args,
                                  ArgStringList &CmdArgs) const {
  CmdArgs.push_back(Args.MakeArgString("-lclang_rt.builtins-" +
                                       getTriple().getArchName()));
}

void baremetal::Linker::ConstructJob(Compilation &C, const JobAction &JA,
                                     const InputInfo &Output,
                                     const InputInfoList &Inputs,
                                     const ArgList &Args,
                                     const char *LinkingOutput) const {
  ArgStringList CmdArgs;

auto &TC = static_cast<const toolchains::BareMetal&>(getToolChain());

AddLinkerInputs(TC, Inputs, Args, CmdArgs, JA);

CmdArgs.push_back("-Bstatic");

CmdArgs.push_back(Args.MakeArgString("-L" + TC.getRuntimesDir()));

Args.AddAllArgs(CmdArgs, {options::OPT_L, options::OPT_T_Group,
                            options::OPT_e, options::OPT_s, options::OPT_t,
                            options::OPT_Z_Flag, options::OPT_r});

if (TC.ShouldLinkCXXStdlib(Args))
    TC.AddCXXStdlibLibArgs(Args, CmdArgs);
  if (!Args.hasArg(options::OPT_nostdlib, options::OPT_nodefaultlibs)) {
    CmdArgs.push_back("-lc");
    CmdArgs.push_back("-lm");

TC.AddLinkRuntimeLib(Args, CmdArgs);
  }

CmdArgs.push_back("-o");
  CmdArgs.push_back(Output.getFilename());

C.addCommand(std::make_unique<Command>(JA, *this, ResponseFileSupport::None(),
                                         Args.MakeArgString(TC.GetLinkerPath()),
                                         CmdArgs, Inputs));
}

003 File Manager

Editing: BareMetal.cpp

Upload File

Create Folder