C Is Not a Low-Level Language (2018)

(queue.acm.org)

64 points | by tosh 3 hours ago

14 comments

  • weitendorf 28 minutes ago
    This is such a pedantic point IMO. C is low level because it makes it very easy to work with machine language/assembly and do stuff like this (LLM assisted example follows):

      int main() {
        __m512i vecA = _mm512_setr_epi32(0,1,2,3,4,5,6,7,8,9,10,11,12,13,14,15);
        __m512i vecB = _mm512_setr_epi32(0,5,10,15,20,25,30,35,40,45,50,55,60,65,70,75);
        unsigned short mask = 0;
    
        __asm__ (
            "vp2intersectd %[B], %[A], %%k2"
            : "=@cck2" (mask)
            : [A] "v" (vecA), [B] "v" (vecB)
            : "k3"
        );
    
        printf("Intersection Mask: 0x%04X\n", mask);
        return 0;
      }
    
    This is something "low level" programmers use very often to realize the benefits of a high-level language while exercising explicit control over using specific hardware instructions (vp2intersectd being an AVX-512 instruction used in highly optimized search algorithm impls).

    Obviously if you rely on implicit behavior from the compiler to optimize your code you are no longer "low level". But if you can quickly and easily drop into machine-level instructions to provide explicit implementation semantics, and the language indeed makes that relatively simple and easy to do, that sure seems "low level" to me

  • bee_rider 1 hour ago
    “Low level language” is one of those terms like “VLSI” (very large scale integration) where they defined it in the 70’s or something, so the academic definition is out-of-sync with what most people would expect.

    This is fine, it’s a term of art and those don’t need to be immediately obvious.

    I don’t like the title of this article for that reason, though. Really a better title would be something like “a modern x86 processor is not a PDP-11.” The subtitle is perfect basically.

    Edit: also IMO it is not really fair to beat up on C for this, the problem is not really one of low-level-ness. A language that actually exposed the complexity of speculative execution and all that could be pretty high level. It would just be harder to read in a linear text editor, right? We’d be better off drawing the dependency graph or something.

  • p0w3n3d 1 minute ago
    C is not a low level language. It's a macro assembler
  • legobmw99 1 hour ago
    I’ve been a fan of this article for years, though it does often make me think that there really aren’t any true low level languages for our super scalar modern CPUs. Does anyone know of any?
    • aDyslecticCrow 1 hour ago
      The article does make an example quite early;

      > GPUs achieve very high performance without any of this logic, at the expense of requiring explicitly parallel programs.

      GPU cores are in some ways closer to "PDP-11", they're either acting as thousands of parallel simple processors, or expose pretty raw instructions for very parallel use-cases.

      • legobmw99 54 minutes ago
        That seems fair, CUDA kernels and shader code do feel like they're at a similar level of abstraction over the hardware as C was to the PDP-11. But I do think there isn't really an equivalent for modern CPU ISAs
        • aDyslecticCrow 38 minutes ago
          Mabie hand-rolling LLVM IR representations would count.
    • jjtheblunt 49 minutes ago
      > really aren’t any true low level languages for our super scalar modern CPUs

      do you mean low level but higher level than assembly language for those processors (like MIPS assembly for an R10k, for example) ?

    • ferguess_k 1 hour ago
      Wondering can we write microcode? That's definitely closer to the metal.
      • wat10000 8 minutes ago
        That was kind of the original idea of RISC. Expose simple instructions that could be implemented without microcode. Push the complexity into the program instead of the microcode. Instead of writing a memory-to-memory add instruction that decomposes into load, load, add, store microcode, you directly write the load, load, add, store.

        This didn’t quite work out in the long term since hardware evolves faster than ISAs. Today’s “maps directly to the hardware” instruction is tomorrow’s “we add more hardware and play tricks to make this faster.” You explode all of the physical registers as logical registers, then a few years later you double the physical registers count and do clever mapping to extract more speed.

        My favorite is the MIPS branch delay slot. Instead of complicated branch prediction to hide latency, expose the pipeline directly to the programmer. And then a couple of hardware generations down the line, the pipeline becomes much longer and more complicated and the CPU is back to playing tricks to hide latency, and the weird branch delay slot remains as essentially a vestige of bygone days.

    • giancarlostoro 1 hour ago
      Probably Mojo, it doesnt just talk to your CPU it also will talk to your GPU bypassing the need for CUDA. Its early days, but I see strong potential in Mojo. Currently its primary focus is GPUs for AI inference, but give it a year or two and it will be really interesting for more than just that.
      • huijzer 26 minutes ago
        Mojo to me seems like a high level language with some additional support for low level control especially around GPUs. A bit like Rust or C but with more streamlined Python integration and more low level GPU (matrices) support.
      • poly2it 56 minutes ago
        But Mojo is a high level language?
    • MrBuddyCasino 1 hour ago
      In what way would exposing the true microcoded out-of-order etc nature of the beast benefit certain tasks?
      • legobmw99 40 minutes ago
        Better control over the async nature of the hardware is part of what makes GPU kernels efficient, but I'm not terribly sure the same thing would be the case on the other side of the PCIe bus.

        But even before you get to out-of-order/speculative execution, I think most languages lack good (i.e. non-intrinsic-based) support for wide registers or anything SIMD related. I know C++ and Rust are both working on this

      • 12_throw_away 32 minutes ago
        It's a good and interesting question, why is it important whether or not it will "benefit certain tasks"? And how would we even know if we haven't tried it?
    • glouwbug 48 minutes ago
      [dead]
    • lelanthran 37 minutes ago
      [flagged]
  • glouwbug 1 hour ago
    Maybe not then, but we basically have our own poor man's template system now:

        #define array(T, N) struct array##T##N { T value[N]; }
    
        void copy(array(int, 32)* x, array(int, 32)* y) {
            *x = *y;
        }
    
        int main() {
            array(int, 32) x;
            array(int, 32) y = { 1, 2, 3, 4 };
            copy(&x, &y);
        }
    
    With (rumors of) lambdas and defer on the way, C is going the way of classic WoW.

    https://en.wikipedia.org/wiki/C29_(C_standard_revision)

    • leptons 1 hour ago
      >C is going the way of classic WoW

      What does this mean?

      • omani 1 hour ago
        it means C is going the way of classic World of Warcraft.
        • mid-kid 54 minutes ago
          What does that mean?
          • glouwbug 23 minutes ago
            WoW released a steady stream of expansions from 2004 to present day. At some point players wanted the old game, so Blizzard released WoW 2004, known as classic, in 2018, and reran the stream of expansions, stopping before any mass enshittification. You can draw the same parallels with C and C++, where C began picking the best from C++ in 1999, 2011, 2023, and soon to be 2029, and carving its own "classic" path.

            We even have our Herb Sutter: Jens Gustedt

    • warmwaffles 1 hour ago
      I remember `defer` being up for consideration for the last consortium but it got yanked. Lambdas would definitely be nice to have.
      • glouwbug 1 hour ago
        Seems like its in C29, but who knows. I've waited since 2009 for just about anything
        • warmwaffles 48 minutes ago
          C29 is shaping up to be some quality of life changes. And it looks like clang has a lot of it implemented already. GCC seems to be implementing some of them. `countof(thing)` seems handy so I don't have to define some constant and use them in both places.
          • glouwbug 30 minutes ago
            Not having to write

                #define len(x) sizeof(x) / sizeof(*x)
            
            Is arguably the feature I've waited for for 20 years
  • jrhey 30 minutes ago
    I’d say assembly is the lowest level programming language we have. You have to balance the abstraction of hardware instructions with being human readable to also qualify as a programming language

    I don’t think byte code qualifies as human readable but it is closer to the metal obviously

  • veqq 1 hour ago
    This is one of my favorite papers; it stole about a year and a half of my time. I still pine for Lisp processors although array languages can now self-host on GPUs, which, APL-pilled, I now feel is better. It'd be so cool (...for compiler writers) to be able to control precisely which kernels stay in which cache levels etc.
  • serbuvlad 24 minutes ago
    C is a low-level language for the current ISAs we have, though not for Itanium.

    So the question is if we really want lower level ISAs. Probably not?

    There are many ways in which our current ISAs are actually thoughtfully optimized for superscalar out-of-order processors. Just look at all of the big differences from 32 bit arm to 64 bit arm, which all exist to make execution faster on superscalar processors.

    And yet they are still perfectly implementable in cheap microcontrollers. The Cortex-A53, available in boards for a little over $15, is a simple 2-wide perfectly in-order design, without a physical register page beyond the ISA register. Basically, it is a simple Pentium-type chip.

    The Apple M chips are some of the most impressive feats of out-of-order superscalar micro-engineering ever. And yet both of these can run the same software with the same ISA. This is enormously valuable.

    I fail to see how any sort of much lower level access to the machine would be portable across price ranges and microarchitecture generations. I also fail to see how it would provide a non-trivial speedup over C code pattern recommendations and targeted extensions (eg. vector extensions).

  • Peteragain 48 minutes ago
    Okay. I like this article and I've thought about it regularly since it last made the rounds here. 1) C is a low level language for a PDP11, or for a single core on a GPU. 2) But what would a low level language look like for an FPGA? Probably verilog. 3) The point worth pursuing however is whether there might be a Hardware agnostic "low level language". 4) yep Haskel by the looks of things. If only I could find the reference.. :-/ There's a set of slides from a crew in Edinburgh doing the history of functional languages. Does any one remember something similar?
    • stephen_cagle 20 minutes ago
      I've never done verilog professionally but I did "Digital Design and Computer Architecture, RISC-V Edition: RISC-V Edition" as an exercise 2 years ago.

      I would say Verilog is very much NOT a low level language.

      Metaphorically, it feels closer to SQL to me. I mean this in that you theoretically tell the system what it should do, and it builds it into the messy real world. However, the reality is that the planner (sql) or linker/placer/router/whatever (verilog) are very good, but you often end up needing to actually fully understand the problem anyway when things don't work in the abstract.

      I know there is https://clash-lang.org/ for Verilog design, which sounds a little like what you are talking about (never really looked at it myself).

    • mathisfun123 10 minutes ago
      > what would a low level language look like for an FPGA? Probably verilog

      Verilog is not a programming language (because FPGAs are not programmed) it's a hardware description language. It's also very lossy (every vendor has reams of coding guides for using it just right with their synthetizer).

  • blastonico 1 hour ago
    In this sense, not even assembly is a low-level language because an instruction may hide what the microcode is actually doing.

    IMHO, C is the lowest level a procedural programming language can get.

  • actionfromafar 1 hour ago
    If anyone was thinking, but in practice it is a low level language, behold Fil-C.
  • EGreg 1 hour ago
    It's just a matter of personal definitions, it seems. Here is an example:

    https://ulanguage.org

    What level would you say this language was? Is it a low-level systems language, or is it also usable for writing web sites?

    • rfgplk 1 hour ago
      Unique language!

      To me the definition of low-level vs high-level strictly comes from the indirection the language runtime provides for you. If the language compiles down to asm, it's low level. It literally does _not_ matter what it looks like. The only other constraint is possibly whether you can manipulate low-level CPU level constructors like memory, albeit it's not necessary. You can take python and write an LLVM frontend for it and it would instantly become a low-level language.

      • bee_rider 12 minutes ago
        I think that would be confusing. Intuitively “low level language” describes the language. Your definition actually describes the nature of the compiler implementation.
  • fsckboy 1 hour ago
    >and even the pre- and post-increment operators cleanly lined up with the PDP-11 addressing modes.

    pre- and post- increment operators cleanly lined up with... the programmer's conceptualization and objectives--the index is/was frequently used in other contexts than loop bounds and indexing. if that's not your conceptualization, don't use that operator. whether you are on a PDP-11 makes no difference.

  • applfanboysbgon 1 hour ago
    This article is so blatantly fallacious I can't even get past the first couple of paragraphs. Perhaps it makes a stronger case later in the article, but the early claims it makes invoke Meltdown/Spectre, eg. speculative execution, and your CPU being more advanced than a PDP-11, and that C doesn't expose modern CPU features like speculative execution, therefore C is not low-level. But assembly doesn't either. You could attempt to make the claim that assembly is no longer a low-level language, but the article explicitly does not do this, instead listing assembly as the low-level extreme that C is being compared against.

    This is embarrassingly bad.

    • mustache_kimono 53 minutes ago
      > You could attempt to make the claim that assembly is no longer a low-level language, but the article explicitly does not do this, instead listing assembly as the low-level extreme that C is being compared against.

      The article mentions assembly once. But it's not an argument about how assembly is "low level" and C isn't, although it may sound like that, upon a first reading, given the article's contentious tone.

      The article is really an argument about how C programmers believe, and constantly state, that they are programming "close to the metal", but what they are really programming is a very fast PDP-11 emulator with lots of implicit behavior.

      Implicit behavior like speculative execution and asynchronous execution and lots and lots of caching.

      • applfanboysbgon 40 minutes ago
        > The article mentions assembly once. But it's not an argument about how assembly is "low level"

        It is, though:

        > Think of programming languages as belonging on a continuum, with assembly at one end

        The article explicitly states that assembly is the end of the continuum, that it is the lowest of the low-level. Therefore, it is not making the argument that assembly is not low-level. But the exact same arguments it makes to distinguish C as not low-level can be applied to assembly. The entire article is based on a fundamental logical error.

        • mustache_kimono 25 minutes ago
          > The article explicitly states

          Again -- I think your impression is the result of the contentious tone of the article. Yes, the article explicitly states:

              "Think of programming languages as belonging on a continuum, with assembly at one end and the interface to the Starship Enterprise’s computer at the other. Low-level languages are “close to the metal,” whereas high-level languages are closer to how humans think."
          
          But then spends the rest of the article debunking this commonly held notion, specifically and explicitly re: C, but also implicitly re: assembly.

          See the very next section "FAST PDP-11 EMULATORS"

              "The root cause of the Spectre and Meltdown vulnerabilities was that processor architects were trying to build not just fast processors, but fast processors that expose the same abstract machine as a PDP-11. This is essential because it allows C programmers to continue in the belief that their language is close to the underlying hardware."
          
          The author obviously knows that assembly suffers from the same abstraction penalty. The author is saying, because C and processor design has been so tightly intertwined, we cannot program "close to the metal" because "the machine" is actually a very fast PDP-11 emulator.

          See also the section "IMAGINING A NON-C PROCESSOR", where the author explicitly discusses alternative processor designs (which would of course require new assembly languages!).

          The author is actually trying something like a reductio on your mental model. When the author states "Think of programming languages as belonging on a continuum", the author is really saying "This is everyone's impression, but ... when you look a little deeper you see the cracks (which are actually contradictions)."

          • applfanboysbgon 11 minutes ago
            At my most charitable, I would give the author credit for knowing that assembly is not low-level by his own definition, but nonetheless intentionally misleads readers who do not know that assembly does not expose speculative execution instructions any more than C does. If the author knew this, and his central premise were that no low-level programming language existed anymore, the article would be titled differently and he wouldn't be making the arguments against C specifically. Really, that would be an entirely different article if written honestly. But this is essentially packaged as clickbait that takes advantage of ignorant readers to make the author sound smarter and more insightful than he really is, and still contains logical errors perpetuated as misinformation to the readers who don't know better. After writing out my charitable interpretation of the author's capabilities, this interpretation only leaves me more disgusted with the article as a writing output.
    • rfgplk 1 hour ago
      > C doesn't expose modern CPU features like speculative execution, therefore C is not low-level

      This is a 100% skill issue of the author, as is always the case. C does expose it fully, except it's implicitly implied by your code rather than explicitly declared. Same with all of the other arguments that always plague these type of articles.

      • jact 43 minutes ago
        Can you elaborate? It’s “implicitly implied” by your code? How is that “exposing it fully” except in the sense that speculative execution is “implicitly implied” in all code targeting the relevant hardware?
    • aDyslecticCrow 45 minutes ago
      > You could attempt to make the claim that assembly is no longer a low-level language

      Assembly expose instructions that C was never meant to work with. Compilers force C to do so anyway. If you had a compiler that converted 8086 x86 assembly to modern x86 or CUDA bytecode; I'd consider that pretty equivalent.

      LLMV intermediate representation is probably more low level (closer to the real compute model it runs on) than that theoretical 8086 x86 compiler.

    • nizmow 1 hour ago
      I think that’s the point.