Link [ NetBSD | NetBSD OpenGrok source search | PR fulltext-search | Summary of daily snapshot builds | history of daily build result | pkgsrc commit viewer ]


   
        usage: [branch:branch] [user:user] [path@revision] keyword [... [-excludekeyword [...]]] (e.g. branch:MAIN sys/arch/arm, if_wm.c@1.234 )




switch to index mode

recent branches: MAIN (1h)  netbsd-10 (17d)  netbsd-9 (17d)  netbsd-8 (22d) 

2024-06-03 04:02:11 UTC Now

2016-02-19 19:25:59 UTC MAIN commitmail json YAML

Don't use #pragma weak to implicitly change argument types.

(joerg)

2016-02-19 19:25:22 UTC MAIN commitmail json YAML

dmu_objset_rename is an alias for dsl_dataset_rename, but differs in
constness of the first argument. Newer clang checks for this and
prohibits it, so just be consistent by constifying the latter.

(joerg)

2016-02-19 18:47:24 UTC MAIN commitmail json YAML

switch powerpc ports to new binutils

(macallan)

2016-02-19 18:38:37 UTC MAIN commitmail json YAML

add cpu_lock

from freqlabs on irc

(pooka)

2016-02-19 17:05:40 UTC MAIN commitmail json YAML

2016-02-19 13:50:37 UTC MAIN commitmail json YAML

PR/50827: Richard Hansen: Fix default variable assignment with arithmetic,
from kre.

(christos)

2016-02-19 13:49:01 UTC MAIN commitmail json YAML

undo accidental commit

(christos)

2016-02-19 13:48:28 UTC MAIN commitmail json YAML

2016-02-19 06:19:06 UTC MAIN commitmail json YAML

Initialize curFile->depending in Parse_SetInput.

(sjg)

2016-02-19 04:18:32 UTC MAIN commitmail json YAML

Explicitly cast between char and unsigned char here.

(riastradh)

2016-02-19 03:54:37 UTC MAIN commitmail json YAML

Need <stdbool.h> for true/false.

(riastradh)

2016-02-19 03:53:47 UTC MAIN commitmail json YAML

Need <stdbool.h> for true/false.

(riastradh)

2016-02-19 03:43:42 UTC MAIN commitmail json YAML

Various housekeeping.

- Include <ufs/lfs/lfs.h> for union lfs_dinode &c.
- Include <string.h> or <sys/systm.h> for memcpy.
- Avoid signedness mismatch in lfs dino accessor for `rdev'.
- Avoid shadowing global `index'.

(riastradh)

2016-02-19 00:11:45 UTC MAIN commitmail json YAML

getBoolean:
We need :U to ensure we get an empty string if knob isn't set.

(sjg)

2016-02-18 23:33:25 UTC MAIN commitmail json YAML

Delete :@ loop iterator when done with it

(sjg)

2016-02-18 20:50:44 UTC MAIN commitmail json YAML

gcc does not pass floating point options to the assembler
by default, because it is afraid that the stricter tests
will break userland code. The new binutils is pickier about
this. Gcc 5.x fixes the issue so for now, set explicitly
the assembler soft-float flags when we build the kernel.
see: https://gcc.gnu.org/bugzilla/show_bug.cgi?id=64569

(macallan)

2016-02-18 20:33:41 UTC MAIN commitmail json YAML

2016-02-18 20:25:09 UTC MAIN commitmail json YAML

Add .export-literal to avoid the need for $$ dance when trying to put
unexpanded variables into environment.

Reviewed by: christos

(sjg)

2016-02-18 18:29:14 UTC MAIN commitmail json YAML

2016-02-18 15:42:44 UTC MAIN commitmail json YAML

Avoid reading one byte past end of array.

Fixes

  acpiout0: brightness levels: [20,25,30,35,40,45,50,55,60,65,70,75,80,85,90,uvm_fault(0xffffffff8133d200, 0xffff80000c1d8000, 1) -> e
  fatal page fault in supervisor mode
  trap type 6 code 0 rip ffffffff803b63d7 cs 8 rflags 10212 cr2 ffff80000c1d8000 ilevel 8 rsp ffffffff816a1b00

(riastradh)

2016-02-18 06:18:58 UTC MAIN commitmail json YAML

2016-02-18 05:40:50 UTC MAIN commitmail json YAML

Actually FALSE as last arg to Var_Subst makes more sense

(sjg)

2016-02-18 05:02:49 UTC MAIN commitmail json YAML

Add support for .dinclude

Like .sinclude missing file will be ignored.
Like .depend stale dependencies will be ignored.
Allows better implementation of auto depend.

Reviewed by: christos
Requested by: Bryan Drewery at FreeBSD.

(sjg)

2016-02-18 05:01:39 UTC MAIN commitmail json YAML

Adapt to new Var_Subst prototype

(sjg)

2016-02-17 20:12:42 UTC MAIN commitmail json YAML

Adapt CI20 HWRNG to synchronous on-demand callback.
Omit needless softint/locking dance.
from riastradh@

(macallan)

2016-02-17 20:11:17 UTC MAIN commitmail json YAML

2016-02-17 20:05:45 UTC MAIN commitmail json YAML

PR/50818: David Binderman: Delete dead code (copied from if_et.c)

(christos)

2016-02-17 20:04:39 UTC MAIN commitmail json YAML

PR/50817: David Binderman: Delete dead code (copy from if_et.c)

(christos)

2016-02-17 20:02:41 UTC MAIN commitmail json YAML

PR/50819: David Binderman: Delete dead code.

(christos)

2016-02-17 20:00:16 UTC MAIN commitmail json YAML

PR/50820: David Binderman: Fail when !(edge|pulse) instead of !edge && edge

(christos)

2016-02-17 19:57:01 UTC MAIN commitmail json YAML

PR/50821: David Binderman: remove "i <" i <

(christos)

2016-02-17 19:54:11 UTC MAIN commitmail json YAML

PR/50822: David Binderman: Fix copy length.

(christos)

2016-02-17 19:52:20 UTC MAIN commitmail json YAML

PR/50823: David Binderman: Limit scanf width

(christos)

2016-02-17 19:51:29 UTC MAIN commitmail json YAML

PR/50824: David Binderman: Limit scanf width

(christos)

2016-02-17 19:47:49 UTC MAIN commitmail json YAML

2016-02-17 19:44:40 UTC MAIN commitmail json YAML

Don't schedule a softint if we have nothing to do.

Some systems seem to have gotten stuck in a softint processing loop
doing nothing and then trying to do it again.  Might fix gson's
frozen qemu/anita sparc autobuilds -- tested on macallan's real sparc
hardware and confirmed to fix at least some freeze at boot.

(riastradh)

2016-02-17 18:51:41 UTC MAIN commitmail json YAML

add a shadowfb update function which endian-swaps 32bit pixels, use if we
have hardware with BGRA pixel format ( like a wrong-endian ARGB framebuffer )
with this applications that use xrender work properly on things like mgx in
32bit colour

(macallan)

2016-02-17 10:52:55 UTC MAIN commitmail json YAML

extend the match function, to match devices from a selection of
manufacturers that use modern Broadcom chips, and which represent
as a vendor-specific device class.

(plunky)

2016-02-17 01:48:36 UTC MAIN commitmail json YAML

Need <sys/mutex.h> for mutex(9).

(riastradh)

2016-02-17 01:48:04 UTC MAIN commitmail json YAML

Caller must have exclusive access to rndsource for rnd_add_data(_sync).

(riastradh)

2016-02-17 01:42:25 UTC MAIN commitmail json YAML

Make hyperentropy rndsource work synchronously, again.

This time for real!  *crosses fingers*

(riastradh)

2016-02-17 01:23:33 UTC MAIN commitmail json YAML

Move entropy_count into the scope where it is used.

Omit now-unused definition.

XXX This code probably shouldn't be under DIAGNOSTIC...  It is
significantly more than just an assertion.

(riastradh)

2016-02-17 01:09:49 UTC MAIN commitmail json YAML

Use real atomics, not atomics faked with membars, for rnd_printing.

(riastradh)

2016-02-17 01:01:42 UTC MAIN commitmail json YAML

Omit needless call to rnd_getmore in rnd_extract_data.

The only remaining caller -- rnd_extract -- already does it.

(riastradh)

2016-02-17 00:57:36 UTC MAIN commitmail json YAML

Omit call to rnd_getmore from rnd_process_events.

There are three cases to consider here:

1. You have on-demand synchronous rndsources, e.g. RDRAND (and you're
willing to use it).  In that case, you'll just use those whenever you
need to extract entropy.  There's no benefit to requesting more from
them when we're entering data into the pool.

2. You have on-demand asynchronous rndsources.  These should continue
trying to feed data to the entropy pool as long as it needs more, so
there's no benefit to requesting more from them when we're entering
data into the pool.

3. You don't have any on-demand rndsources.  Then rnd_getmore does
nothing, so there's no benefit to calling it.

ok tls

(riastradh)

2016-02-17 00:49:28 UTC MAIN commitmail json YAML

Match various Apple USB Bluetooth controllers.

From mlelstv.

(riastradh)

2016-02-17 00:48:57 UTC MAIN commitmail json YAML

2016-02-17 00:46:17 UTC MAIN commitmail json YAML

Add various USB Bluetooth controllers.

From mlelstv.

(riastradh)

2016-02-17 00:43:43 UTC MAIN commitmail json YAML

Add rnd_add_data_sync for synchronous on-demand rndsource callbacks.

Avoids lock recursion in rndsinks:

rndsink user holds lock
calls rndsink_request
calls rnd_getmore
calls an rndsource callback
calls rnd_add_data
calls rnd_process_events
calls rndsinks_distribute
calls rndsink callback
acquires rndsink user lock.

This can happen only before the rnd_process_events softint is
established, but that's enough to cause a problem and is the main
reason why all our HWRNG drivers are so byzantine (soon to be
fixed!).

ok tls

(riastradh)

2016-02-17 00:01:23 UTC MAIN commitmail json YAML

Cast uint8_t to uint32_t before shifting left by 24.

Otherwise this is undefined behaviour unless int is 32-bit and the
uint8_t value happens to be <=127.

(riastradh)

2016-02-16 23:07:58 UTC MAIN commitmail json YAML

Need <sys/queue.h> for LIST_ENTRY and <sys/null.h> for NULL.

(riastradh)

2016-02-16 22:53:14 UTC MAIN commitmail json YAML

2016-02-16 19:29:51 UTC MAIN commitmail json YAML

- don't set _GNU_SOURCE. We are not supposed to make decisions for others.
- don't special-case wcsdup()
From Ingo Schwarze.

(christos)

2016-02-16 19:11:25 UTC MAIN commitmail json YAML

get rid of bool_t (Ingo Schwarze)

(christos)

2016-02-16 19:08:41 UTC MAIN commitmail json YAML

2016-02-16 15:54:15 UTC MAIN commitmail json YAML

2016-02-16 15:53:48 UTC MAIN commitmail json YAML

2016-02-16 14:08:25 UTC MAIN commitmail json YAML

2016-02-16 14:07:47 UTC MAIN commitmail json YAML

2016-02-16 14:06:06 UTC MAIN commitmail json YAML

2016-02-16 14:04:58 UTC MAIN commitmail json YAML

include explicitly errno.h since we use it.

(christos)

2016-02-16 14:04:24 UTC MAIN commitmail json YAML

No need to include "sys.h" from here; it is included from config.h

(christos)

2016-02-16 08:41:32 UTC MAIN commitmail json YAML

In xennet_xenbus_detach(), remove the event handler early (just after
xennet_stop()) so that we don't get events while slepping (e.g.
in softint_disestablish()) when some structures have already been
freed.
Problem reported and patch tested by Rohan Desai.

(bouyer)

2016-02-16 07:51:13 UTC MAIN commitmail json YAML

Re-enable the TT support that existed previously.

(skrll)

2016-02-16 05:14:31 UTC MAIN commitmail json YAML

Reduced INSTALL kernel size.

(nonaka)

2016-02-16 01:31:26 UTC MAIN commitmail json YAML

Remove workaround for GATEWAY

The workaround was introduced because lltable/llentry uses rwlock
but it may be executed in hardware interrupt due to fast forward.
Now we don't run fast forward in hardware interrupt anymore, so
we can remove the workaround.

(ozaki-r)

2016-02-15 23:36:30 UTC MAIN commitmail json YAML

2016-02-15 22:53:38 UTC MAIN commitmail json YAML

OpenBSD term.c rev. 1.7 2002/11/29 20:13:39 deraadt
spelling

(christos)

2016-02-15 22:48:59 UTC MAIN commitmail json YAML

OpenBSD readline.c rev. 1.14 2015/02/06 23:21:58 millert
use SIZE_MAX

(christos)

2016-02-15 22:37:54 UTC MAIN commitmail json YAML

cardbus autoconf uses cardbus_attach_args, not isapnp_attach_args.

(riastradh)

2016-02-15 21:58:38 UTC MAIN commitmail json YAML

OpenBSD readline.c rev. 1.13 2015/01/13 08:33:12 reyk
rl_set_keyboard_input_timeout() for readline 4.2 compat

(christos)

2016-02-15 21:56:35 UTC MAIN commitmail json YAML

OpenBSD eln.c rev. 1.3 2011/11/27 21:46:44 pascal
kill a C++-style comment

(christos)

2016-02-15 21:38:07 UTC MAIN commitmail json YAML

Compile with WIDECHAR the same way the main Makefile does (Ingo Schwarze)

(christos)

2016-02-15 21:35:52 UTC MAIN commitmail json YAML

Don't free getline memory (Ingo Schwarze).

(christos)

2016-02-15 20:58:02 UTC MAIN commitmail json YAML

allllllexander the greeeaaaaat, his name struck fear into hearts of men!

...but let's conquer that fear and give ol' alex a consistent and
correct date of death.

(he died of fever in baaaaaabylooooooonnnn)

(snj)

2016-02-15 20:35:59 UTC MAIN commitmail json YAML

Use KASSERTs supported by CTASSERTs, not __builtin_unreachable.

pcc has no __builtin_unreachable, and this is clearer anyway.

(riastradh)

2016-02-15 20:33:18 UTC MAIN commitmail json YAML

2016-02-15 19:36:35 UTC MAIN commitmail json YAML

2016-02-15 19:00:42 UTC MAIN commitmail json YAML

Fix building of IPv4-Mapped IPv6 addresses.

As discussed on tech-net@ use in6_sin_2_v4mapsin6() to build mapped
addresses.

(rtr)

2016-02-15 17:35:39 UTC MAIN commitmail json YAML

forgot one fgetln define

(christos)

2016-02-15 16:14:39 UTC MAIN commitmail json YAML

2016-02-15 15:56:33 UTC MAIN commitmail json YAML

Fix function name, no functional change.
Found by Travis Paul, (see PR/50786), thanks for reporting!

(mbalmer)

2016-02-15 15:53:45 UTC MAIN commitmail json YAML

Use getline for better portability.

(christos)

2016-02-15 15:37:20 UTC MAIN commitmail json YAML

OpenBSD tokenizer.c rev. 1.8 2003/08/11 18:21:40 deraadt
don't increase amax on realloc failure

(christos)

2016-02-15 15:35:03 UTC MAIN commitmail json YAML

OpenBSD term.c rev. 1.13 2009/12/11 18:58:59 jacekm
fix two memory leaks

(christos)

2016-02-15 15:30:50 UTC MAIN commitmail json YAML

Change the test for the size of encoded buffer to include the NULL, from
OpenBSD; no functional change.

(christos)

2016-02-15 15:29:25 UTC MAIN commitmail json YAML

OpenBSD sig.c rev. 1.6 2001/12/06 04:26:00 deraadt
save and restore errno in signal handler

(christos)

2016-02-15 15:26:48 UTC MAIN commitmail json YAML

Use fparseln to avoid newline hacks.

(christos)

2016-02-15 15:18:01 UTC MAIN commitmail json YAML

use fparseln() to avoid needing to deal with missing \n in the last line
and also to handle comments automatically.

(christos)

2016-02-15 14:59:38 UTC MAIN commitmail json YAML

This needs _KERNTYPES on some platforms.

(christos)

2016-02-15 14:59:03 UTC MAIN commitmail json YAML

Reduce code duplication.

Split creation of IPv4-Mapped IPv6 addresses into its own function
and use it.

No functional change intended.  As posted to tech-net@

(rtr)

2016-02-15 13:25:12 UTC MAIN commitmail json YAML

Add missing closing ) and line continuation for mknative

(martin)

2016-02-15 11:07:48 UTC MAIN commitmail json YAML

Avoid strict alias violation for VAX

(martin)

2016-02-15 08:08:04 UTC MAIN commitmail json YAML

Run if_link_state_change in softint

if_link_state_change can execute the network stack that is expected to
not run in hardware interrupt (at least now), however network drivers
may call it in hardware interrupt. Avoid that by introducing a new
softint for if_link_state_change.

The original patch is provided by mlelstv@ and tweaked a bit by me.

Should fix PR kern/50602.

(ozaki-r)

2016-02-15 01:11:41 UTC MAIN commitmail json YAML

Simplify bridge(4)

Thanks to introducing softint-based if_input, the entire bridge code now
never run in hardware interrupt context. So we can simplify the code.

- Remove spin mutexes
  - They were needed because some code of bridge could run in
    hardware interrupt context
  - We now need only an adaptive mutex for each shared object
    (a member list and a forwarding table)
- Remove pktqueue
  - bridge_input is already in softint, using another softint
    (for bridge_forward) is useless
  - Packet distribution should be down at device drivers

(ozaki-r)

2016-02-14 23:47:57 UTC MAIN commitmail json YAML

remove duplicated #include of <netinet/in.h>

(rtr)

2016-02-14 21:13:34 UTC MAIN commitmail json YAML

sun4v: add breakpoint trap entry to the sun4v trap table

(palle)

2016-02-14 19:54:21 UTC MAIN commitmail json YAML

2016-02-14 19:11:20 UTC MAIN commitmail json YAML

Remove extra stray break missed by Christos when committing PR 50783.

(dholland)

2016-02-14 19:08:10 UTC MAIN commitmail json YAML

Restore the local change
  -gcc: internal compiler error: Killed (program cc1plus)
  +gcc: internal compiler error: Killed (program cc1plus received signal 9)
which was lost in an update somewhere after netbsd-6.

This clarification was found in the past to significantly reduce the
number of bug reports caused by people running out of swap, such as
(most likely) seen again today in PR 50802.

XXX: pullup-7

(dholland)

2016-02-14 19:00:04 UTC MAIN commitmail json YAML

2016-02-14 18:12:31 UTC MAIN commitmail json YAML

Add missing va_end, from David Binderman in PR 50798.

(dholland)

2016-02-14 18:11:16 UTC MAIN commitmail json YAML

Add missing va_end, from David Binderman in PR 50797.

(dholland)

2016-02-14 18:09:51 UTC MAIN commitmail json YAML

Add missing va_list, from David Binderman in PR 50796.

XXX: this file and arch/arc/stand/boot/disk.c are cutpaste clones.

(dholland)

2016-02-14 18:07:49 UTC MAIN commitmail json YAML

Add missing va_end; PR 50795 from David Binderman.

(dholland)

2016-02-14 18:05:31 UTC MAIN commitmail json YAML

2016-02-14 18:04:47 UTC MAIN commitmail json YAML

Add missing va_end(). PR 50794 from David Binderman.

(dholland)

2016-02-14 18:01:45 UTC MAIN commitmail json YAML

Add missing va_end. PR 50793 from David Binderman.

(dholland)

2016-02-14 17:06:24 UTC MAIN commitmail json YAML

From Ingo Schwarze:

el_getc() for the WIDECHAR case, that is, the version in eln.c.
For a UTF-8 locale, it is broken in four ways:

1. If the character read is outside the ASCII range, the function
    does an undefined cast from wchar_t to char.  Even if wchar_t
    is internally represented as UCS-4, that is wrong and dangerous
    because characters beyond codepoint U+0255 get their high bits
    truncated, meaning that perfectly valid printable Unicode
    characters get mapped to arbitrary bytes, even the ASCII escape
    character for some Unicode characters.  But wchar_t need not
    be implemented in terms of UCS-4, so the outcome of this function
    is undefined for any and all input.

2. If insufficient space is available for the result, the function
    fails to detect failure and returns garbage rather than -1 as
    specified in the documentation.

3. The documentation says that errno will be set on failure, but
    that doesn't happen either in the above case.

4. Even for ASCII characters, the results may be wrong if wchar_t
    is not using UCS-4.

(christos)

2016-02-14 14:49:34 UTC MAIN commitmail json YAML

From Ingo Schwarze:

As we have seen before, "histedit.h" can never get rid of including
the <wchar.h> header because using the data types defined there is
deeply ingrained in the public interfaces of libedit.

Now POSIX unconditionally requires that <wchar.h> defines the type
wint_t.  Consequently, it can be used unconditionally, no matter
whether WIDECHAR is active or not.  Consequently, the #define Int
is pointless.

Note that removing it is not gratuitious churn.  Auditing for
integer signedness problems is already hard when only fundamental
types like "int" and "unsigned" are involved.  It gets very hard
when types come into the picture that have platform-dependent
signedness, like "char" and "wint_t".  Adding yet another layer
on top, changing both the signedness and the width in a platform-
dependent way, makes auditing yet harder, which IMHO is really
dangerous.  Note that while removing the #define, i already found
one bug caused by this excessive complication - in the function
re_putc() in refresh.c.  If WIDECHAR was defined, it printed an
Int = wint_t value with %c.  Fortunately, that bug only affects
debugging, not production.  The fix is contained in the patch.

With WIDECHAR, this doesn't change anything.  For the case without
WIDECHAR, i checked that none of the places wants to store values
that might not fit in wint_t.

This only changes internal interfaces; public ones remain unchanged.

(christos)

2016-02-14 14:47:48 UTC MAIN commitmail json YAML

From Ingo Schwartze:

Next step:  Remove #ifdef'ing in read_char(), in the same style
as we did for setlocale(3) in el.c.

A few remarks are required to explain the choices made.

* On first sight, handling mbrtowc(3) seems a bit less trivial
  than handling setlocale(3) because its prototype uses the data
  type mbstate_t from <wchar.h>.  However, it turns out that
  "histedit.h" already includes <wchar.h> unconditionally (i don't
  like headers including other headers, but that ship has sailed,
  people are by now certainly used to the fact that including
  "histedit.h" doesn't require including <wchar.h> before), and
  "histedit.h" is of course included all over the place.  So from
  that perspective, there is no problem with using mbrtowc(3)
  unconditionally ever for !WIDECHAR.

* However, <wchar.h> also defines the mbrtowc(3) prototype,
  so we cannot just #define mbrtowc away, or including the header
  will break.  It would also be a bad idea to porovide a local
  implementation of mbrtowc() and hope that it overrides the one
  in libc.  Besides, the required prototype is subtly different:
  While mbrtowc(3) takes "wchar_t *" as its first argument, we
  need a function that takes "Char *".  So unfortunately, we have
  to keep a ct_mbrtowc #define, at least until we can maybe get
  rid of "Char *" in the more remote future.

* After getting rid of the #else clause in read_char(), we can
  pull "return 1;" into the default: clause.  After that, we can
  get rid of the ugly "goto again_lastbyte;" and just "break;".
  As a bonus, that also gets rid of the ugly CONSTCOND.

* While here, delete the unused ct_mbtowc() from chartype.h.

(christos)

2016-02-14 10:56:23 UTC MAIN commitmail json YAML

Update for latest dwc2 dist

(skrll)

2016-02-14 10:53:30 UTC MAIN commitmail json YAML

2016-02-14 10:34:09 UTC MAIN commitmail json YAML

Fix DWC2_READ_4 in dwc2_sample_frrem which is unused

(skrll)

2016-02-14 03:41:18 UTC MAIN commitmail json YAML

Map the same mmio size as Linux does.

Unlikely to have practical consequences -- just reduces differences
in behaviour from upstream, to rule them out.

(riastradh)

2016-02-14 03:06:06 UTC MAIN commitmail json YAML

Fix bus_space_subregion error branch.

Return error code, not 0 (!), on bus_space_subregion failure.

In answer to `XXX error branch' comment: if nouveau_barobj_ctor
fails, then the caller will call nouveau_barobj_dtor too.  So there's
no leak here.

Unlikely to fix any observed bugs with nouveau -- there's no error
branch in the Linux side here.  But maybe it will catch some other
bug earlier.

(riastradh)

2016-02-13 23:12:34 UTC MAIN commitmail json YAML

2016-02-13 21:37:12 UTC MAIN commitmail json YAML

2016-02-13 19:53:23 UTC MAIN commitmail json YAML

2016-02-13 08:44:22 UTC MAIN commitmail json YAML

Pass all unicast addresses if it is promisc mode.

(hikaru)

2016-02-13 08:05:07 UTC MAIN commitmail json YAML

Make all packets are enqueued into queue 0.
queue 7 is not default, it is caused by the filter tables.
The fields are including queue number, not bitfields.
So MVXPE_DF_QUEUE_ALL (b111) means queue 7.

And also, pass all unicast addresses if it is promisc mode.
MVXPE_PXC_UPM is working in almost cases,
but this change is needed for some cases; bridging frames through inter units,
using products have consecutive MAC addresses.

(hikaru)

2016-02-13 06:44:22 UTC MAIN commitmail json YAML

Fix typo in sysctls.

(hikaru)

2016-02-13 06:33:21 UTC MAIN commitmail json YAML

Count up if_{opackets,oerrors,ierrors,collisions}.
And also "MAC Transmit Error" is tx error, not rx.

(hikaru)

2016-02-13 06:12:46 UTC MAIN commitmail json YAML

2016-02-13 06:02:31 UTC MAIN commitmail json YAML

Preserve rx csum bad flags.

(hikaru)

2016-02-13 05:47:39 UTC MAIN commitmail json YAML

Fix mitake, disable SERDES error interrupts again.

(hikaru)

2016-02-13 05:44:01 UTC MAIN commitmail json YAML

Don't use RXTX intr that is excess and requires another IRQ handler,
and disable SERDES error interrupts.

(hikaru)

2016-02-13 05:21:11 UTC MAIN commitmail json YAML

Correct bus_dmamap_sync operaion.

(hikaru)

2016-02-13 03:33:02 UTC MAIN commitmail json YAML

Correct locks and missing breaks.

(hikaru)

2016-02-12 17:23:21 UTC MAIN commitmail json YAML

Avoid c99 for now.

(christos)

2016-02-12 15:36:08 UTC MAIN commitmail json YAML

GC IGNORE_EXTCHARS and simplify code (Ingo Schwarze)

(christos)

2016-02-12 15:11:09 UTC MAIN commitmail json YAML

From Ingo Schwarze:

If CHARSET_IS_UTF8 is not set, read_char() is broken in a large
number of ways:

1. The isascii(3) check can yield false positives.  If a string in
    an arbitrary encoding contains a byte in the range 0..127,
    that does not at all imply that it forms a character all by
    itself, and even less that it represents the same character
    as in ASCII.  Consequently, read_char() may return characters
    the user never typed.
    Even if the encoding is not state dependent, the assumption that
    bytes in the range 0..127 represent ASCII characters is broken.
    Consider UTF-16, for example.

2. The reverse problem can also occur.  In an arbitrary encoding,
    there is no guarantee that a character that can be represented
    by ASCII is represented by a seven-bit byte, and even less by
    the same byte as in ASCII.
    Even for single-byte encodings, these assumptions are broken.
    Consider the ISO 646 national variants, for example.
    Consequently, the current code is insufficient to keep ASCII
    characters working even for single-byte encodings.

3. The condition "++cbp != 1" can never trigger (because initially,
    cbp is 0, and the code can only go back up via the final goto,
    which has another cbp = 0 right before it) and it has no effect
    (because cbp isn't used afterwards).

4. bytes = ct_mbtowc(cp, cbuf, cbp) is broken.  If this returns -1,
    the code assumes that is can just call mbtowc(3) again for later
    input bytes.  In some implementations, that may even be broken
    for state-independent encodings, but trying again after mbtowc(3)
    failure certainly produces completely erratic and meaningless
    results in state-dependent encodings.

5. The assignment "*cp = (Char)(unsigned char)cbuf[0]" is
    completely bogus.  Even if the byte cbuf[0] represents a
    character all by itself, which it usually will not, whether
    or not the cast produces the desired result depends on the
    internal representation of wchar_t in the C library, which
    the application program can know nothing about.  Even for ASCII
    in the C/POSIX locale, an ASCII character other than '\0' ==
    L'\0' == 0 need not have the same numeric value as a char and
    as a wchar_t.

To summarize, this code only works if all of the following
conditions hold:

- The encoding is a single-byte encoding.
- ASCII is a subset of the encoding.
- The implementation of mbtowc(3) in the C library does not
  require re-initialization after encoding errors.
- The implementation of wchar_t in the C library uses the
  same numerical values as ASCII.

Otherwise, it silently produces wrong results.

The simplest way to fix this is to just use the same code as for
UTF-8 (right above).  Of course, that causes functional changes
but that shouldn't matter since current behaviour is undefined.

The patch below provides the following improvements:

- It works for all stateless single-byte encodings, no matter
  whether they are somehow related to ASCII, no matter how
  mb[r]towc(3) are internally implemented, and no matter how
  wchar_t is internally represented.
- Instead of producing unpredictable and definitely wrong
  results for non-UTF-8 multibyte characters, it behaves in
  a well-defined way: It aborts input processing, sets errno,
  and returns failure.
  Note that short of providing full support for arbitrary locales,
  it is impossible to do better.  We cannot know whether a given
  unsupported locale is state-dependent, and for a state-dependent
  locale, it makes no sense to retry parsing after an encoding
  error, so the best we can do is abort processing for *any*
  unsupported multi-byte character.
- Note that single-byte characters in arbitrary state-independent
  locales still work, even in locales that may potentially also
  contain multibyte characters, as long as those don't occur in
  input.  I'm not sure whether any such locales exist in practice...

Tested with UTF-8 and C/POSIX on OpenBSD.  Also tested that in the
C/POSIX locale, non-ASCII bytes get through unmangled.  You may
wish to test with ISO-LATIN on NetBSD if NetBSD supports that.

----
Also use a constant for meta to avoid warnings.

(christos)

2016-02-12 09:24:15 UTC MAIN commitmail json YAML

Fix the bitmask of MVXPE_PMACC0_FRAMESIZELIMIT. It did no harm.

(hikaru)

2016-02-12 08:36:29 UTC MAIN commitmail json YAML

2016-02-12 08:36:08 UTC MAIN commitmail json YAML

add several NVIDIA geforce and NVS cards.

(mrg)

2016-02-12 05:32:47 UTC MAIN commitmail json YAML

2016-02-11 20:53:06 UTC MAIN commitmail json YAML

support screen blanking and hw cursor

(macallan)

2016-02-11 19:21:04 UTC MAIN commitmail json YAML

2016-02-11 19:10:18 UTC MAIN commitmail json YAML

remove unused wrapper (Ingo Schwarze)

(christos)

2016-02-11 16:08:47 UTC MAIN commitmail json YAML

Remove utf8_islead() mbrtowc() handles this just fine (Ingo Schwarze)

(christos)

2016-02-11 13:36:00 UTC MAIN commitmail json YAML

texinfo-6.1 and grep-2.23 out.

(wiz)

2016-02-11 04:51:44 UTC MAIN commitmail json YAML

Pass a sensible device state pointer to nouveau suspend/resume ops.

Gives nouveau half a chance of suspending and resuming -- not that it
works on my test laptop yet, but it's a start.

(riastradh)

2016-02-11 04:43:32 UTC MAIN commitmail json YAML

Set nouveau to a more reasonable debug level.

Match the compile-time and default run-time settings in Linux.

(riastradh)

2016-02-11 04:42:15 UTC MAIN commitmail json YAML

Try xf86-video-nouveau for nvidia devices by default.

Fall back to nv (and then vesa and then wsfb) if it doesn't work.

(riastradh)

2016-02-11 02:23:44 UTC MAIN commitmail json YAML

switch to 32bit colour in WSDISPLAYIO_MODE_MAPPED, now X with wsfb will work
Not optimal though - for some reason the framebuffer's endianness in 32bit
colour is wrong and I have no idea (yet) how to change that, so many apps
using xrender will crash.

(macallan)

2016-02-10 17:10:47 UTC MAIN commitmail json YAML

2016-02-10 06:30:23 UTC MAIN commitmail json YAML

Don't share struct work, instead have one per softc

Pointed out by riastradh@

(ozaki-r)

2016-02-09 20:44:26 UTC MAIN commitmail json YAML

use pcpp front end rather than libexec/cpp directly, since commandline
options may not be handled by the latter

(plunky)

2016-02-09 20:42:45 UTC MAIN commitmail json YAML

add pcpp binary, now in pcc-20160208. Also, p++ in debug set

(plunky)

2016-02-09 20:40:46 UTC MAIN commitmail json YAML

2016-02-09 20:37:32 UTC MAIN commitmail json YAML

2016-02-09 14:43:16 UTC MAIN commitmail json YAML

2016-02-09 14:14:02 UTC MAIN commitmail json YAML

Document file format better. From Travis Paul and Matthew Bauer.

Bump date.
Addresses PR 50787.

(wiz)

2016-02-09 12:53:17 UTC MAIN commitmail json YAML

Add more #warning message 'Please use mvxpe instead of this'.

(kiyohara)

2016-02-09 12:48:06 UTC MAIN commitmail json YAML

Clear ATAC_CAP_DATA32, if dev is atabus@wdc@pcmcia@aupcmcia.  It is 32-bit transfers are not supported.

(kiyohara)

2016-02-09 10:20:03 UTC MAIN commitmail json YAML

Actually, descsz should not contain the padding. The note still needs to
be padded out.

(skrll)

2016-02-09 08:32:12 UTC MAIN commitmail json YAML

Introduce softint-based if_input

This change intends to run the whole network stack in softint context
(or normal LWP), not hardware interrupt context. Note that the work is
still incomplete by this change; to that end, we also have to softint-ify
if_link_state_change (and bpf) which can still run in hardware interrupt.

This change softint-ifies at ifp->if_input that is called from
each device driver (and ieee80211_input) to ensure Layer 2 runs
in softint (e.g., ether_input and bridge_input). To this end,
we provide a framework (called percpuq) that utlizes softint(9)
and percpu ifqueues. With this patch, rxintr of most drivers just
queues received packets and schedules a softint, and the softint
dequeues packets and does rest packet processing.

To minimize changes to each driver, percpuq is allocated in struct
ifnet for now and that is initialized by default (in if_attach).
We probably have to move percpuq to softc of each driver, but it's
future work. At this point, only wm(4) has percpuq in its softc
as a reference implementation.

Additional information including performance numbers can be found
in the thread at tech-kern@ and tech-net@:
http://mail-index.netbsd.org/tech-kern/2016/01/14/msg019997.html

Acknowledgment: riastradh@ greatly helped this work.
Thank you very much!

(ozaki-r)

2016-02-08 21:08:03 UTC MAIN commitmail json YAML

Preserve the .text section alignment

(skrll)

2016-02-08 18:18:19 UTC MAIN commitmail json YAML

Allocate struct cpu_info dynamically.  Saves quite a lot of BSS in the
common case and reduces rump kernel memory requirements by 10% or more
in really tiny deployments.

(pooka)

2016-02-08 17:18:43 UTC MAIN commitmail json YAML

UTF-8 fixes from Ingo Schwarze:

1. Assume that errno is non-zero when entering read_char()
    and that read(2) returns 0 (indicating end of file).
    Then, the code will clear errno before returning.
    (Obviously, the statement "errno = 0" is almost always
    a bug unless there is save_errno = errno right before it
    and the previous value is properly restored later,
    in all reachable code paths.)

2. When encountering an invalid byte sequence, the code discards
    all following bytes until MB_LEN_MAX overflows; consider, for
    example, 0xc2 immediately followed by a few valid ASCII bytes.
    Three of those ASCII bytes will be discarded.

3. On a POSIX system, EILSEQ will always be set after reading a
    valid (yes, valid, not invalid!) UTF-8 character.  The reason
    is that mbtowc(3) will first be called with a length limit
    (third argument) of 1, which will fail, return -1, and - on
    a POSIX system - set errno to EILSEQ.
    This third bug is mitigated a bit because i couldn't find any
    system that actually conforms to POSIX in this respect:  None
    of OpenBSD, NetBSD, FreeBSD, Solaris 11, and glibc set errno
    when an incomplete character is passed to mbtowc(3), even though
    that is required by POSIX.
    Anyway, that mbtowc(3) bug will be fixed at least in OpenBSD
    after release unlock, so it would be good to fix this bug in
    libedit before fixing the bug in mbtowc(3).

How can these three bugs be fixed?

1. As far as i understand it, the intention of the bogus errno = 0
    is to undo the effects of failing system calls in el_wset(),
    sig_set(), and read__fixio() if the subsequent read(2) indicates
    end of file.  So, restoring errno has to be moved right after
    read__fixio().  Of course, neither 0 nor e is the right value
    to restore: 0 is wrong if errno happened to be set on entry, e
    would be wrong because if one read(2) fails but a second attempt
    succeeds after read__fixio(), errno should not be touched.  So,
    the errno to be restored in this case has to be saved before
    calling read(2) for the first time.

2. Solving the second issue requires distinguishing invalid and
    incomplete characters, but that is impossible with the function
    mbtowc(3) because it returns -1 in both cases and sets errno
    to EILSEQ in both cases (once properly implemented).

    It is vital that each input character is processed right away.
    It is not acceptable to wait for the next input character before
    processing the previous one because this is an interactive
    library, not a batch system.  Consequently, the only situation
    where it is acceptable to wait for the next byte without first
    processing the previous one(s) is when the previous one(s) form
    an incomplete sequence that can be continued to form a valid
    character.

    Consequently, short of reimplementing a full UTF-8 state machine
    by hand, the only correct way forward is to use mbrtowc(3).
    Even then, care is needed to always have the state object
    properly initialized before using it, and to not discard a valid
    ASCII or UTF-8 lead byte if it happens to follow an invalid
    sequence.

3. Fortunately, solution 2. also solves issue 3. as a side effect,
    by no longer using mbtowc(3) in the first place.

(christos)

2016-02-08 16:44:46 UTC MAIN commitmail json YAML

PR/50783: David Binderman: Indent switch properly, add missing break.

(christos)

2016-02-08 16:42:04 UTC MAIN commitmail json YAML

PR/50784: David Binderman: Add missing braces, this is not python.

(christos)

2016-02-08 16:27:51 UTC MAIN commitmail json YAML

PR/50785: David Binderman: Remove dead code.

(christos)

2016-02-08 11:59:39 UTC MAIN commitmail json YAML

Fix .note.netbsd.march by ensuring correct padding

(skrll)

2016-02-08 10:39:09 UTC MAIN commitmail json YAML

Remove the .SUNW_ctf sections when converting form ELF -> a.out by
updating OBJCOPY_ELF2AOUT_FLAGS

(skrll)

2016-02-08 05:27:24 UTC MAIN commitmail json YAML

2016-02-07 21:03:49 UTC MAIN commitmail json YAML

2016-02-07 18:41:25 UTC MAIN commitmail json YAML

Use IPL_NONE for pserialized lock.  Assert sleepable.  (OOPS.)

(riastradh)

2016-02-07 14:31:22 UTC MAIN commitmail json YAML

2016-02-07 14:06:04 UTC MAIN commitmail json YAML

2016-02-07 10:46:08 UTC MAIN commitmail json YAML

Add the copyright notice which was missing from my initial version.

(jandberg)

2016-02-07 05:03:36 UTC MAIN commitmail json YAML

Fix signing of in-memory data with SSH keys

(agc)

2016-02-06 22:48:07 UTC MAIN commitmail json YAML

In module_do_load(), consolidate checking for a pre-existing module,
and return a single error value EEXIST.  When making a recursive
call (to load required modules), treat a pre-existing module as
success.

Without this change, when a module was loaded by specific request
(as opposed to being loaded as a requirement of some other module),
we would always load the module from the file-system, and then
after making various sanity/compatability checks we would destroy
the new copy if there was a pre-existing copy.

Fixes PR kern/40764

XXX Note that if the module exists, we bypass all of the various
XXX "compatability" checks, including whether or not the existing
XXX module is of any particular class!  (In the previous code, we
XXX checked to see if the newly-loaded copy had the correct class,
XXX but not the pre-existing copy, which could have been loaded
XXX from a different path/filename.)

(pgoyette)

2016-02-06 21:23:09 UTC MAIN commitmail json YAML

use sizeof() and array notation.

(christos)

2016-02-06 20:23:39 UTC MAIN commitmail json YAML

No <immintrin.h> for pcc even on x86.

(riastradh)

2016-02-06 20:21:56 UTC MAIN commitmail json YAML

METEORGSIGNAL and METEORSFMT overlap with dtrace, prefer the latter.

(joerg)

2016-02-06 20:20:19 UTC MAIN commitmail json YAML

2016-02-06 20:19:28 UTC MAIN commitmail json YAML

2016-02-06 19:33:07 UTC MAIN commitmail json YAML

2016-02-06 19:22:01 UTC MAIN commitmail json YAML

Override default LIB_PATH for i386 emulation. Unlike older binutils, we
now have to check the emulation and not that the target as the change
otherwise leaks into the native 64bit linker scripts as well.

(joerg)

2016-02-06 19:20:49 UTC MAIN commitmail json YAML

We don't want to target-specific search directories on NetBSD in the
linker scripts, they just add noise.

(joerg)

2016-02-06 18:23:26 UTC MAIN commitmail json YAML

2016-02-06 18:20:00 UTC MAIN commitmail json YAML

SDT is not a disease. Use const consistently.

(joerg)

2016-02-06 16:58:31 UTC MAIN commitmail json YAML

Back out unintended changes committed with last.

(riz)

2016-02-06 16:56:23 UTC MAIN commitmail json YAML

Don't test dtrace-related variables until after they've been set.

(riz)

2016-02-06 15:36:36 UTC MAIN commitmail json YAML

Don't do _BSD_SIZE_T_ dance here.  Use <stddef.h> in userland.

This file is used in tools, where _BSD_SIZE_T_ is unreliable.  In the
kernel, <sys/types.h> will define size_t anyway.  Outside the kernel,
<stddef.h> is the standard way to get size_t.

(riastradh)

2016-02-06 14:11:58 UTC MAIN commitmail json YAML

2016-02-06 10:40:58 UTC MAIN commitmail json YAML

2016-02-06 10:35:59 UTC MAIN commitmail json YAML

2016-02-06 02:40:49 UTC MAIN commitmail json YAML

2016-02-06 02:39:51 UTC MAIN commitmail json YAML

Convert bool to target type before shift.

(riastradh)

2016-02-06 02:39:18 UTC MAIN commitmail json YAML

Avoid shadowing global `min'.

(riastradh)

2016-02-06 01:59:55 UTC MAIN commitmail json YAML

2016-02-06 01:51:39 UTC MAIN commitmail json YAML

Avoid shadowing global `max' from libkern.

(riastradh)

2016-02-06 00:31:58 UTC MAIN commitmail json YAML

Don't return void.

Caught by pcc.  Thanks, pcc!

(riastradh)

2016-02-05 23:49:26 UTC MAIN commitmail json YAML

2016-02-05 23:46:40 UTC MAIN commitmail json YAML

2016-02-05 23:45:44 UTC MAIN commitmail json YAML

2016-02-05 20:39:50 UTC MAIN commitmail json YAML

Need nbtool_config.h for __dead in tools.

(riastradh)

2016-02-05 19:56:00 UTC MAIN commitmail json YAML

Need nbtools_config.h for __unused.

Fixes

.../src/tools/ctfmerge/../../external/cddl/osnet/dist/tools/ctf/common/list.c:73:47: error: expected ';', ',' or ')' before '__unused'
list_defcmp(void *d1, void *d2, void *private __unused)
                                              ^~~~~~~~

on non-NetBSD systems, where <assert.h>, <stdlib.h>, <stdio.h>, and
<sys/types.h> don't define __unused.

(riastradh)